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 "core/knobs.h"
  28
  29 #if (defined(FORCE_WINDOWS) || defined(_WIN32)) && !defined(FORCE_LINUX)
  30
  31 #define SWR_API __cdecl
  32
  33 #ifndef _CRT_SECURE_NO_WARNINGS
  34 #define _CRT_SECURE_NO_WARNINGS
  35 #endif
  36
  37 #ifndef NOMINMAX
  38 #define NOMINMAX
  39 #endif
  40 #include "Windows.h"
  41 #include <intrin.h>
  42 #include <cstdint>
  43
  44 #define OSALIGN(RWORD, WIDTH) __declspec(align(WIDTH)) RWORD
  45 #define THREAD __declspec(thread)
  46 #define INLINE __forceinline
  47 #define DEBUGBREAK __debugbreak()
  48
  49 #define PRAGMA_WARNING_PUSH_DISABLE(...) \
  50         __pragma(warning(push));\
  51         __pragma(warning(disable:__VA_ARGS__));
  52
  53 #define PRAGMA_WARNING_POP() __pragma(warning(pop))
  54
  55 #if defined(_WIN32)
  56 #if defined(_WIN64)
  57 #define BitScanForwardSizeT BitScanForward64
  58 #define _mm_popcount_sizeT _mm_popcnt_u64
  59 #else
  60 #define BitScanForwardSizeT BitScanForward
  61 #define _mm_popcount_sizeT _mm_popcnt_u32
  62 #endif
  63 #endif
  64
  65 #elif defined(FORCE_LINUX) || defined(__linux__) || defined(__gnu_linux__)
  66
  67 #define SWR_API
  68
  69 #include <stdlib.h>
  70 #include <string.h>
  71 #include <X11/Xmd.h>
  72 #include <x86intrin.h>
  73 #include <stdint.h>
  74 #include <sys/types.h>
  75 #include <unistd.h>
  76 #include <sys/stat.h>
  77
  78 typedef void                    VOID;
  79 typedef void*           LPVOID;
  80 typedef CARD8                   BOOL;
  81 typedef wchar_t                 WCHAR;
  82 typedef uint16_t                UINT16;
  83 typedef int                             INT;
  84 typedef unsigned int    UINT;
  85 typedef uint32_t                UINT32;
  86 typedef uint64_t                UINT64;
  87 typedef int64_t             INT64;
  88 typedef void*                   HANDLE;
  89 typedef float                   FLOAT;
  90 typedef int                         LONG;
  91 typedef CARD8               BYTE;
  92 typedef unsigned char   UCHAR;
  93 typedef unsigned int    DWORD;
  94
  95 #undef FALSE
  96 #define FALSE 0
  97
  98 #undef TRUE
  99 #define TRUE 1
 100
 101 #define OSALIGN(RWORD, WIDTH) RWORD __attribute__((aligned(WIDTH)))
 102 #define THREAD __thread
 103 #ifndef INLINE
 104 #define INLINE __inline
 105 #endif
 106 #define DEBUGBREAK asm ("int $3")
 107 #define __cdecl
 108 #define __declspec(X)
 109
 110 #define GCC_VERSION (__GNUC__ * 10000 \
 111                      + __GNUC_MINOR__ * 100 \
 112                      + __GNUC_PATCHLEVEL__)
 113
 114 #if !defined(__clang__) && (__GNUC__) && (GCC_VERSION < 40500)
 115 inline
 116 uint64_t __rdtsc()
 117 {
 118     long low, high;
 119     asm volatile("rdtsc" : "=a"(low), "=d"(high));
 120     return (low | ((uint64_t)high << 32));
 121 }
 122 #endif
 123
 124 #ifndef __clang__
 125 // Intrinsic not defined in gcc
 126 static INLINE
 127 void _mm256_storeu2_m128i(__m128i *hi, __m128i *lo, __m256i a)
 128 {
 129     _mm_storeu_si128((__m128i*)lo, _mm256_castsi256_si128(a));
 130     _mm_storeu_si128((__m128i*)hi, _mm256_extractf128_si256(a, 0x1));
 131 }
 132 #endif
 133
 134 inline
 135 unsigned char _BitScanForward(unsigned long *Index, unsigned long Mask)
 136 {
 137     *Index = __builtin_ctz(Mask);
 138     return (Mask != 0);
 139 }
 140
 141 inline
 142 unsigned char _BitScanForward(unsigned int *Index, unsigned int Mask)
 143 {
 144     *Index = __builtin_ctz(Mask);
 145     return (Mask != 0);
 146 }
 147
 148 inline
 149 unsigned char _BitScanReverse(unsigned long *Index, unsigned long Mask)
 150 {
 151     *Index = __builtin_clz(Mask);
 152     return (Mask != 0);
 153 }
 154
 155 inline
 156 unsigned char _BitScanReverse(unsigned int *Index, unsigned int Mask)
 157 {
 158     *Index = __builtin_clz(Mask);
 159     return (Mask != 0);
 160 }
 161
 162 inline
 163 void *_aligned_malloc(unsigned int size, unsigned int alignment)
 164 {
 165     void *ret;
 166     if (posix_memalign(&ret, alignment, size))
 167     {
 168         return NULL;
 169     }
 170     return ret;
 171 }
 172
 173 inline
 174 unsigned char _bittest(const LONG *a, LONG b)
 175 {
 176     return ((*(unsigned *)(a) & (1 << b)) != 0);
 177 }
 178
 179 #define GetCurrentProcessId getpid
 180
 181 #define CreateDirectory(name, pSecurity) mkdir(name, 0777)
 182
 183 #if defined(_WIN32)
 184 static inline
 185 unsigned int _mm_popcnt_u32(unsigned int v)
 186 {
 187     return __builtin_popcount(v);
 188 }
 189 #endif
 190
 191 #define _aligned_free free
 192 #define InterlockedCompareExchange(Dest, Exchange, Comparand) __sync_val_compare_and_swap(Dest, Comparand, Exchange)
 193 #define InterlockedExchangeAdd(Addend, Value) __sync_fetch_and_add(Addend, Value)
 194 #define InterlockedDecrement(Append) __sync_sub_and_fetch(Append, 1)
 195 #define InterlockedIncrement(Append) __sync_add_and_fetch(Append, 1)
 196 #define _ReadWriteBarrier() asm volatile("" ::: "memory")
 197 #define __stdcall
 198
 199 #define PRAGMA_WARNING_PUSH_DISABLE(...)
 200 #define PRAGMA_WARNING_POP()
 201
 202 #else
 203
 204 #error Unsupported OS/system.
 205
 206 #endif
 207
 208 // Universal types
 209 typedef BYTE        KILOBYTE[1024];
 210 typedef KILOBYTE    MEGABYTE[1024];
 211 typedef MEGABYTE    GIGABYTE[1024];
 212
 213 #define OSALIGNLINE(RWORD) OSALIGN(RWORD, 64)
 214 #if KNOB_SIMD_WIDTH == 8
 215 #define OSALIGNSIMD(RWORD) OSALIGN(RWORD, 32)
 216 #endif
 217
 218 #include "common/swr_assert.h"
 219
 220 #endif//__SWR_OS_H__