KonstantinSeurer
/
mesa
1
0
Fork 0
Code Issues Pull Requests Packages Projects Releases Wiki Activity

swr/rast: vmask() implementations for KNL 

Reviewed-by: Bruce Cherniak <bruce.cherniak@intel.com>
This commit is contained in:
Tim Rowley 2017-07-27 14:56:46 -05:00
parent c18d91ca9a
commit 39ed8e297c
1 changed files with 14 additions and 0 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

14
src/gallium/drivers/swr/rasterizer/common/simdlib_512_avx512_knights.inl
View File

@ -132,6 +132,20 @@
}
#define SIMD_IWRAPPER_2I(op) SIMD_IWRAPPER_2I_(op, op)
private:
static SIMDINLINE Integer vmask(__mmask8 m)
{
return _mm512_mask_set1_epi64(_mm512_setzero_si512(), m, -1LL);
}
static SIMDINLINE Integer vmask(__mmask32 m)
{
return _mm512_mask_set1_epi16(_mm512_setzero_si512(), m, -1);
}
static SIMDINLINE Integer vmask(__mmask64 m)
{
return _mm512_mask_set1_epi8(_mm512_setzero_si512(), m, -1);
}
public:
SIMD_WRAPPERI_2_(and_ps, and_epi32); // return a & b (float treated as int)
SIMD_WRAPPERI_2_(andnot_ps, andnot_epi32); // return (~a) & b (float treated as int)