NeroReflex/mesa
1
0
Fork 0
Code Issues Pull requests Projects Releases Packages Wiki Activity

swr/rast: fix invalid sign masks in avx512 simdlib code

Browse source 
Should be 0x80000000 instead of 0x8000000.

Cc: mesa-stable@lists.freedesktop.org
Reviewed-by: Bruce Cherniak <bruce.cherniak@intel.com>
This commit is contained in:
Tim Rowley 2018-01-04 10:08:48 -06:00
parent 76daa30e4a
commit 396c006d90
3 changed files with 3 additions and 3 deletions
Download patch file Download diff file Expand all files Collapse all files

2
src/gallium/drivers/swr/rasterizer/common/simdlib_128_avx512.inl
View file

@ -270,7 +270,7 @@ static SIMDINLINE Float SIMDCALL mask_i32gather_ps(Float old, float const* p, In
{
__mmask16 m = 0xf;
m = _mm512_mask_test_epi32_mask(m, _mm512_castps_si512(__conv(mask)),
_mm512_set1_epi32(0x8000000));
_mm512_set1_epi32(0x80000000));
return __conv(_mm512_mask_i32gather_ps(
__conv(old),
m,

2
src/gallium/drivers/swr/rasterizer/common/simdlib_256_avx512.inl
View file

@ -271,7 +271,7 @@ static SIMDINLINE Float SIMDCALL mask_i32gather_ps(Float old, float const* p, In
{
__mmask16 m = 0xff;
m = _mm512_mask_test_epi32_mask(m, _mm512_castps_si512(__conv(mask)),
_mm512_set1_epi32(0x8000000));
_mm512_set1_epi32(0x80000000));
return __conv(_mm512_mask_i32gather_ps(
__conv(old),
m,

2
src/gallium/drivers/swr/rasterizer/common/simdlib_512_avx512.inl
View file

@ -540,7 +540,7 @@ static SIMDINLINE uint32_t SIMDCALL movemask_pd(Double a)
}
static SIMDINLINE uint32_t SIMDCALL movemask_ps(Float a)
{
__mmask16 m = _mm512_test_epi32_mask(castps_si(a), set1_epi32(0x8000000));
__mmask16 m = _mm512_test_epi32_mask(castps_si(a), set1_epi32(0x80000000));
return static_cast<uint32_t>(m);
}