OpenHarmony/third_party_mesa3d
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity

swr/rast: fix movemask_ps / movemask_pd on AVX512

Browse Source 
Reviewed-by: Bruce Cherniak <bruce.cherniak@intel.com>
This commit is contained in:
Tim Rowley
2017-07-20 17:06:14 -05:00
parent f253798205
commit eddbd781af
1 changed files with 7 additions and 2 deletions
Download Patch File Download Diff File Expand all files Collapse all files

9
src/gallium/drivers/swr/rasterizer/common/simdlib_512_avx512.inl
View File

@@ -554,15 +554,20 @@ static SIMDINLINE uint64_t SIMDCALL movemask_epi8(Integer a)
static SIMDINLINE uint32_t SIMDCALL movemask_pd(Double a)
{
__mmask8 m = _mm512_test_epi64_mask(castpd_si(a), set1_epi32(-1));
__mmask8 m = _mm512_test_epi64_mask(castpd_si(a), set1_epi64(0x8000000000000000LL));
return static_cast<uint32_t>(m);
}
static SIMDINLINE uint32_t SIMDCALL movemask_ps(Float a)
{
__mmask16 m = _mm512_test_epi32_mask(castps_si(a), set1_epi32(-1));
__mmask16 m = _mm512_test_epi32_mask(castps_si(a), set1_epi32(0x8000000));
return static_cast<uint32_t>(m);
}
static SIMDINLINE Integer SIMDCALL set1_epi64(long long i) // return i (all elements are same value)
{
return _mm512_set1_epi64(i);
}
static SIMDINLINE Integer SIMDCALL set1_epi32(int i) // return i (all elements are same value)
{
return _mm512_set1_epi32(i);