src/gallium/drivers/swr/rasterizer/common/os.h

   1 /****************************************************************************
   2 * Copyright (C) 2014-2015 Intel Corporation.   All Rights Reserved.
   3 *
   4 * Permission is hereby granted, free of charge, to any person obtaining a
   5 * copy of this software and associated documentation files (the "Software"),
   6 * to deal in the Software without restriction, including without limitation
   7 * the rights to use, copy, modify, merge, publish, distribute, sublicense,
   8 * and/or sell copies of the Software, and to permit persons to whom the
   9 * Software is furnished to do so, subject to the following conditions:
  10 *
  11 * The above copyright notice and this permission notice (including the next
  12 * paragraph) shall be included in all copies or substantial portions of the
  13 * Software.
  14 *
  15 * THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
  16 * IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
  17 * FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.  IN NO EVENT SHALL
  18 * THE AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
  19 * LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING
  20 * FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS
  21 * IN THE SOFTWARE.
  22 ****************************************************************************/
  23
  24 #ifndef __SWR_OS_H__
  25 #define __SWR_OS_H__
  26
  27 #include <cstddef>
  28 #include "core/knobs.h"
  29
  30 #if (defined(FORCE_WINDOWS) || defined(_WIN32)) && !defined(FORCE_LINUX)
  31
  32 #define SWR_API __cdecl
  33
  34 #ifndef NOMINMAX
  35 #define NOMINMAX
  36 #endif
  37 #include "Windows.h"
  38 #include <intrin.h>
  39 #include <cstdint>
  40
  41 #define OSALIGN(RWORD, WIDTH) __declspec(align(WIDTH)) RWORD
  42 #define THREAD __declspec(thread)
  43 #define INLINE __forceinline
  44 #define DEBUGBREAK __debugbreak()
  45
  46 #define PRAGMA_WARNING_PUSH_DISABLE(...) \
  47     __pragma(warning(push));\
  48     __pragma(warning(disable:__VA_ARGS__));
  49
  50 #define PRAGMA_WARNING_POP() __pragma(warning(pop))
  51
  52 static inline void *AlignedMalloc(size_t _Size, size_t _Alignment)
  53 {
  54     return _aligned_malloc(_Size, _Alignment);
  55 }
  56
  57 static inline void AlignedFree(void* p)
  58 {
  59     return _aligned_free(p);
  60 }
  61
  62 #if defined(_WIN64)
  63 #define BitScanReverseSizeT BitScanReverse64
  64 #define BitScanForwardSizeT BitScanForward64
  65 #define _mm_popcount_sizeT _mm_popcnt_u64
  66 #else
  67 #define BitScanReverseSizeT BitScanReverse
  68 #define BitScanForwardSizeT BitScanForward
  69 #define _mm_popcount_sizeT _mm_popcnt_u32
  70 #endif
  71
  72 #elif defined(FORCE_LINUX) || defined(__linux__) || defined(__gnu_linux__)
  73
  74 #define SWR_API
  75
  76 #include <stdlib.h>
  77 #include <string.h>
  78 #include <x86intrin.h>
  79 #include <stdint.h>
  80 #include <sys/types.h>
  81 #include <unistd.h>
  82 #include <sys/stat.h>
  83 #include <stdio.h>
  84
  85 typedef void            VOID;
  86 typedef void*           LPVOID;
  87 typedef int             INT;
  88 typedef unsigned int    UINT;
  89 typedef void*           HANDLE;
  90 typedef int             LONG;
  91 typedef unsigned int    DWORD;
  92
  93 #undef FALSE
  94 #define FALSE 0
  95
  96 #undef TRUE
  97 #define TRUE 1
  98
  99 #define OSALIGN(RWORD, WIDTH) RWORD __attribute__((aligned(WIDTH)))
 100 #define THREAD __thread
 101 #ifndef INLINE
 102 #define INLINE __inline
 103 #endif
 104 #define DEBUGBREAK asm ("int $3")
 105 #if !defined(__CYGWIN__)
 106 #ifndef __cdecl
 107 #define __cdecl
 108 #endif
 109 #ifndef __stdcall
 110 #define __stdcall
 111 #endif
 112 #define __declspec(X)
 113 #endif
 114
 115 #define GCC_VERSION (__GNUC__ * 10000 \
 116                      + __GNUC_MINOR__ * 100 \
 117                      + __GNUC_PATCHLEVEL__)
 118
 119 #if !defined(__clang__) && (__GNUC__) && (GCC_VERSION < 40500)
 120 inline
 121 uint64_t __rdtsc()
 122 {
 123     long low, high;
 124     asm volatile("rdtsc" : "=a"(low), "=d"(high));
 125     return (low | ((uint64_t)high << 32));
 126 }
 127 #endif
 128
 129 #ifndef __clang__
 130 // Intrinsic not defined in gcc
 131 static INLINE
 132 void _mm256_storeu2_m128i(__m128i *hi, __m128i *lo, __m256i a)
 133 {
 134     _mm_storeu_si128((__m128i*)lo, _mm256_castsi256_si128(a));
 135     _mm_storeu_si128((__m128i*)hi, _mm256_extractf128_si256(a, 0x1));
 136 }
 137 #endif
 138
 139 inline
 140 unsigned char _BitScanForward(unsigned long *Index, unsigned long Mask)
 141 {
 142     *Index = __builtin_ctz(Mask);
 143     return (Mask != 0);
 144 }
 145
 146 inline
 147 unsigned char _BitScanForward(unsigned int *Index, unsigned int Mask)
 148 {
 149     *Index = __builtin_ctz(Mask);
 150     return (Mask != 0);
 151 }
 152
 153 inline
 154 unsigned char _BitScanReverse(unsigned long *Index, unsigned long Mask)
 155 {
 156     *Index = __builtin_clz(Mask);
 157     return (Mask != 0);
 158 }
 159
 160 inline
 161 unsigned char _BitScanReverse(unsigned int *Index, unsigned int Mask)
 162 {
 163     *Index = __builtin_clz(Mask);
 164     return (Mask != 0);
 165 }
 166
 167 inline
 168 void *AlignedMalloc(unsigned int size, unsigned int alignment)
 169 {
 170     void *ret;
 171     if (posix_memalign(&ret, alignment, size))
 172     {
 173         return NULL;
 174     }
 175     return ret;
 176 }
 177
 178 inline
 179 unsigned char _bittest(const LONG *a, LONG b)
 180 {
 181     return ((*(unsigned *)(a) & (1 << b)) != 0);
 182 }
 183
 184 static inline
 185 void AlignedFree(void* p)
 186 {
 187     free(p);
 188 }
 189
 190 #define GetCurrentProcessId getpid
 191 #define GetCurrentThreadId gettid
 192
 193 #define CreateDirectory(name, pSecurity) mkdir(name, 0777)
 194
 195 #define InterlockedCompareExchange(Dest, Exchange, Comparand) __sync_val_compare_and_swap(Dest, Comparand, Exchange)
 196 #define InterlockedExchangeAdd(Addend, Value) __sync_fetch_and_add(Addend, Value)
 197 #define InterlockedDecrement(Append) __sync_sub_and_fetch(Append, 1)
 198 #define InterlockedDecrement64(Append) __sync_sub_and_fetch(Append, 1)
 199 #define InterlockedIncrement(Append) __sync_add_and_fetch(Append, 1)
 200 #define _ReadWriteBarrier() asm volatile("" ::: "memory")
 201
 202 #define PRAGMA_WARNING_PUSH_DISABLE(...)
 203 #define PRAGMA_WARNING_POP()
 204
 205 #else
 206
 207 #error Unsupported OS/system.
 208
 209 #endif
 210
 211 // Universal types
 212 typedef uint8_t     KILOBYTE[1024];
 213 typedef KILOBYTE    MEGABYTE[1024];
 214 typedef MEGABYTE    GIGABYTE[1024];
 215
 216 #define OSALIGNLINE(RWORD) OSALIGN(RWORD, 64)
 217 #define OSALIGNSIMD(RWORD) OSALIGN(RWORD, KNOB_SIMD_BYTES)
 218
 219 #include "common/swr_assert.h"
 220
 221 #endif//__SWR_OS_H__