/external/mesa3d/src/gallium/drivers/swr/rasterizer/common/ |
D | simdlib_types.hpp | 42 #define SIMDCALL __vectorcall macro 46 #define SIMDCALL macro 156 SIMDINLINE Float& SIMDCALL operator[](const int i) { return v[i]; } in operator []() 157 SIMDINLINE Float const& SIMDCALL operator[](const int i) const { return v[i]; } in operator []() 158 SIMDINLINE Vec4& SIMDCALL operator=(Vec4 const& in) in operator =() 174 SIMDINLINE Float& SIMDCALL operator=(__m128 in) in operator =() 179 SIMDINLINE Float& SIMDCALL operator=(Float const& in) in operator =() 184 SIMDINLINE SIMDCALL operator __m128() const { return v; } in operator __m128() 193 SIMDINLINE Integer& SIMDCALL operator=(__m128i in) in operator =() 198 SIMDINLINE Integer& SIMDCALL operator=(Integer const& in) in operator =() [all …]
|
D | simdlib_512_avx512.inl | 53 static SIMDINLINE Float SIMDCALL op(Float a) { return intrin(a); } 58 static SIMDINLINE Float SIMDCALL op(Float a, Float b) { return _mm512_##intrin(a, b); } 62 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 69 static SIMDINLINE Double SIMDCALL op(Double a, Double b) { return _mm512_##op(a, b); } 73 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 81 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 88 static SIMDINLINE Float SIMDCALL op(Float a, Float b, Float c) { return _mm512_##op(a, b, c); } 91 static SIMDINLINE Integer SIMDCALL op(Integer a) { return _mm512_##op(a); } 93 static SIMDINLINE Integer SIMDCALL op(SIMD256Impl::Integer a) { return _mm512_##op(a); } 96 static SIMDINLINE Integer SIMDCALL op(SIMD128Impl::Integer a) { return _mm512_##op(a); } [all …]
|
D | simdlib_128_avx.inl | 32 static SIMDINLINE Float SIMDCALL op(Float a) { return _mm_##op(a); } 35 static SIMDINLINE Float SIMDCALL op(Float a, Float b) { return _mm_##op(a, b); } 38 static SIMDINLINE Double SIMDCALL op(Double a, Double b) { return _mm_##op(a, b); } 42 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 49 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 55 static SIMDINLINE Float SIMDCALL op(Float a, Float b, Float c) { return _mm_##op(a, b, c); } 58 static SIMDINLINE Integer SIMDCALL op(Integer a) { return _mm_##op(a); } 62 static SIMDINLINE Integer SIMDCALL op(Integer a) \ 69 static SIMDINLINE Integer SIMDCALL op(Integer a, Integer b) { return intrin(a, b); } 72 static SIMDINLINE Integer SIMDCALL op(Integer a, Integer b) { return _mm_##op(a, b); } [all …]
|
D | simdlib_256_avx.inl | 34 static SIMDINLINE Float SIMDCALL op(Float const& a) { return _mm256_##op(a); } 37 static SIMDINLINE Float SIMDCALL op(Float const& a, Float const& b) \ 43 static SIMDINLINE Double SIMDCALL op(Double const& a, Double const& b) \ 50 static SIMDINLINE Float SIMDCALL op(Float const& a, Float const& b) \ 57 static SIMDINLINE Double SIMDCALL op(Double const& a, Double const& b) \ 63 static SIMDINLINE Float SIMDCALL op(Float const& a, Float const& b, Float const& c) \ 69 static SIMDINLINE Integer SIMDCALL op(Integer const& a) { return _mm256_##op(a); } 72 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 78 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 85 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ [all …]
|
D | simdlib_512_emu.inl | 35 static SIMDINLINE Float SIMDCALL op(Float const& a) \ 44 static SIMDINLINE Float SIMDCALL op(Float const& a, Float const& b) \ 54 static SIMDINLINE Float SIMDCALL op(Float const& a, Float const& b) \ 64 static SIMDINLINE Float SIMDCALL op(Float const& a, Float const& b) \ 73 static SIMDINLINE Float SIMDCALL op(Float const& a, Float const& b, Float const& c) \ 82 static SIMDINLINE Integer SIMDCALL op(Integer const& a) \ 91 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 101 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 111 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 121 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ [all …]
|
D | simdlib_512_avx512_knights.inl | 33 static SIMDINLINE Float SIMDCALL op(Float a) { return intrin(a); } 38 static SIMDINLINE Float SIMDCALL op(Float a, Float b) { return _mm512_##intrin(a, b); } 42 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 49 static SIMDINLINE Double SIMDCALL op(Double a, Double b) { return _mm512_##op(a, b); } 53 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 61 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 68 static SIMDINLINE Float SIMDCALL op(Float a, Float b, Float c) { return _mm512_##op(a, b, c); } 71 static SIMDINLINE Integer SIMDCALL op(Integer a) { return _mm512_##op(a); } 73 static SIMDINLINE Integer SIMDCALL op(SIMD256Impl::Integer a) { return _mm512_##op(a); } 76 static SIMDINLINE Integer SIMDCALL op(SIMD128Impl::Integer a) { return _mm512_##op(a); } [all …]
|
D | simdlib_512_avx512_core.inl | 33 static SIMDINLINE Float SIMDCALL op(Float a) { return intrin(a); } 38 static SIMDINLINE Float SIMDCALL op(Float a, Float b) { return _mm512_##intrin(a, b); } 42 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 49 static SIMDINLINE Double SIMDCALL op(Double a, Double b) { return _mm512_##op(a, b); } 53 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 61 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 68 static SIMDINLINE Float SIMDCALL op(Float a, Float b, Float c) { return _mm512_##op(a, b, c); } 71 static SIMDINLINE Integer SIMDCALL op(Integer a) { return _mm512_##op(a); } 73 static SIMDINLINE Integer SIMDCALL op(SIMD256Impl::Integer a) { return _mm512_##op(a); } 76 static SIMDINLINE Integer SIMDCALL op(SIMD128Impl::Integer a) { return _mm512_##op(a); } [all …]
|
D | simdlib_128_avx512.inl | 64 static SIMDINLINE Float SIMDCALL op(Float a) \ 72 static SIMDINLINE Float SIMDCALL op(Float a) \ 79 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 87 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 93 static SIMDINLINE Float SIMDCALL op(Float a, Float b, Float c) \ 101 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 107 static SIMDINLINE Integer SIMDCALL op(Integer a) \ 115 static SIMDINLINE Integer SIMDCALL op(Integer a) \ 122 static SIMDINLINE Integer SIMDCALL op(Integer a, Integer b) \ 130 static SIMDINLINE Integer SIMDCALL op(Integer a, Integer b) \ [all …]
|
D | simdlib_256_avx512.inl | 64 static SIMDINLINE Float SIMDCALL op(Float a) \ 72 static SIMDINLINE Float SIMDCALL op(Float a) \ 79 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 87 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 93 static SIMDINLINE Float SIMDCALL op(Float a, Float b, Float c) \ 101 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 107 static SIMDINLINE Integer SIMDCALL op(Integer a) \ 115 static SIMDINLINE Integer SIMDCALL op(Integer a) \ 122 static SIMDINLINE Integer SIMDCALL op(Integer a, Integer b) \ 130 static SIMDINLINE Integer SIMDCALL op(Integer a, Integer b) \ [all …]
|
D | simdlib_128_avx512_core.inl | 37 static SIMDINLINE Float SIMDCALL op(Float a) \ 45 static SIMDINLINE Float SIMDCALL op(Float a) \ 52 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 60 static SIMDINLINE Float SIMDCALL op(Float a, Float b) \ 66 static SIMDINLINE Float SIMDCALL op(Float a, Float b, Float c) \ 73 static SIMDINLINE Double SIMDCALL op(Double a) \ 81 static SIMDINLINE Double SIMDCALL op(Double a) \ 88 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 96 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 102 static SIMDINLINE Integer SIMDCALL op(Integer a) \ [all …]
|
D | simdlib_256_avx2.inl | 36 static SIMDINLINE Integer SIMDCALL op(Integer const& a) { return _mm256_##op(a); } 39 static SIMDINLINE Integer SIMDCALL op(Integer const& a) \ 46 static SIMDINLINE Integer SIMDCALL op(Integer const& a) \ 53 static SIMDINLINE Integer SIMDCALL op(Integer const& a) \ 59 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 65 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 72 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 79 static SIMDINLINE Integer SIMDCALL op(Integer const& a, Integer const& b) \ 88 static SIMDINLINE Float SIMDCALL fmadd_ps(Float const& a, 143 static SIMDINLINE Float SIMDCALL srlisi_ps(Float const& a) [all …]
|
D | simdlib_256_avx512_core.inl | 37 static SIMDINLINE Double SIMDCALL op(Double a) \ 45 static SIMDINLINE Double SIMDCALL op(Double a) \ 52 static SIMDINLINE Double SIMDCALL op(Double a, Double b) \ 59 static SIMDINLINE Integer SIMDCALL op(Integer a) \ 69 static SIMDINLINE Integer SIMDCALL op(Integer a) \ 78 static SIMDINLINE Integer SIMDCALL op(Integer a, Integer b) \ 105 static SIMDINLINE uint32_t SIMDCALL movemask_epi8(Integer a)
|
D | simdlib_128_avx2.inl | 36 static SIMDINLINE Float SIMDCALL op(Float a, Float b, Float c) { return _mm_##op(a, b, c); } 41 static SIMDINLINE Integer SIMDCALL sllv_epi32(Integer vA, Integer vB) // return a << b (uint32) 46 static SIMDINLINE Integer SIMDCALL srlv_epi32(Integer vA, Integer vB) // return a >> b (uint32) 52 static SIMDINLINE Float SIMDCALL 60 static SIMDINLINE Float SIMDCALL
|
/external/mesa3d/src/gallium/drivers/swr/rasterizer/core/ |
D | format_conversion.h | 37 INLINE void SIMDCALL LoadSOA(const uint8_t* pSrc, Vec4<SIMD_T>& dst) in LoadSOA() 83 INLINE void SIMDCALL LoadSOA(const uint8_t* pSrc, simdvector& dst) in LoadSOA() 89 INLINE void SIMDCALL LoadSOA(const uint8_t* pSrc, simd16vector& dst) in LoadSOA() 100 INLINE Float<SIMD_T> SIMDCALL Clamp(Float<SIMD_T> const& v, uint32_t Component) in Clamp() 148 INLINE simdscalar SIMDCALL Clamp(simdscalar const& v, uint32_t Component) in Clamp() 154 INLINE simd16scalar SIMDCALL Clamp(simd16scalar const& v, uint32_t Component) in Clamp() 165 INLINE Float<SIMD_T> SIMDCALL Normalize(Float<SIMD_T> const& vComp, uint32_t Component) in Normalize() 177 INLINE simdscalar SIMDCALL Normalize(simdscalar const& vComp, uint32_t Component) in Normalize() 183 INLINE simd16scalar SIMDCALL Normalize(simd16scalar const& vComp, uint32_t Component) in Normalize() 194 INLINE void SIMDCALL StoreSOA(const Vec4<SIMD_T>& src, uint8_t* pDst) in StoreSOA() [all …]
|
D | clip.cpp | 240 void SIMDCALL ClipRectangles_simd16(DRAW_CONTEXT* pDC, in ClipRectangles_simd16() 264 void SIMDCALL ClipTriangles_simd16(DRAW_CONTEXT* pDC, in ClipTriangles_simd16() 288 void SIMDCALL ClipLines_simd16(DRAW_CONTEXT* pDC, in ClipLines_simd16() 312 void SIMDCALL ClipPoints_simd16(DRAW_CONTEXT* pDC, in ClipPoints_simd16()
|
D | format_types.h | 47 static void SIMDCALL storeSOA(uint8_t* pDst, simd16scalar const& src) = delete; 66 static void SIMDCALL storeSOA(uint8_t* pDst, simd16scalar const& src) { return; } 147 static void SIMDCALL storeSOA(uint8_t* pDst, simd16scalar const& src) 268 static void SIMDCALL storeSOA(uint8_t* pDst, simd16scalar const& src) 385 static void SIMDCALL storeSOA(uint8_t* pDst, simd16scalar const& src) 488 static void SIMDCALL storeSOA(uint8_t* pDst, simd16scalar const& src) 538 static void SIMDCALL storeSOA(uint8_t* pDst, simd16scalar const& src) 926 inline static simd16scalar SIMDCALL fastpow(simd16scalar const& value) 948 inline static simd16scalar SIMDCALL pow512_4(simd16scalar const& arg) 971 inline static simd16scalar SIMDCALL powf_wrapper(const simd16scalar& base, float exp) [all …]
|
D | frontend.h | 431 void SIMDCALL BinPoints_simd16(DRAW_CONTEXT* pDC, 439 void SIMDCALL BinLines_simd16(DRAW_CONTEXT* pDC,
|
D | clip.h | 1329 void SIMDCALL ClipRectangles_simd16(DRAW_CONTEXT* pDC, 1337 void SIMDCALL ClipTriangles_simd16(DRAW_CONTEXT* pDC, 1345 void SIMDCALL ClipLines_simd16(DRAW_CONTEXT* pDC, 1353 void SIMDCALL ClipPoints_simd16(DRAW_CONTEXT* pDC,
|
D | binner.cpp | 350 uint32_t SIMDCALL EarlyRasterizer(DRAW_CONTEXT* pDC, in EarlyRasterizer() 667 void SIMDCALL BinTrianglesImpl(DRAW_CONTEXT* pDC, in BinTrianglesImpl() 1229 void SIMDCALL BinTriangles_simd16(DRAW_CONTEXT* pDC, in BinTriangles_simd16() 1655 void SIMDCALL BinPoints_simd16(DRAW_CONTEXT* pDC, in BinPoints_simd16() 1895 void SIMDCALL BinLinesImpl(DRAW_CONTEXT* pDC, in BinLinesImpl() 1963 void SIMDCALL BinLines_simd16(DRAW_CONTEXT* pDC, in BinLines_simd16()
|
D | context.h | 236 typedef void(SIMDCALL* PFN_PROCESS_PRIMS_SIMD16)(DRAW_CONTEXT* pDC,
|