diff options
| author | Tim Rowley <[email protected]> | 2018-01-04 10:08:48 -0600 |
|---|---|---|
| committer | Tim Rowley <[email protected]> | 2018-01-04 13:35:17 -0600 |
| commit | 396c006d907b023f9b187db618ee2a6e4e1b8a85 (patch) | |
| tree | 8e8798b910954bfe6c9bcb0742ff142f6ad34719 /src/gallium | |
| parent | 76daa30e4a0d3dfe04c5b79fcdfba17fb1656ccd (diff) | |
swr/rast: fix invalid sign masks in avx512 simdlib code
Should be 0x80000000 instead of 0x8000000.
Cc: [email protected]
Reviewed-by: Bruce Cherniak <[email protected]>
Diffstat (limited to 'src/gallium')
3 files changed, 3 insertions, 3 deletions
diff --git a/src/gallium/drivers/swr/rasterizer/common/simdlib_128_avx512.inl b/src/gallium/drivers/swr/rasterizer/common/simdlib_128_avx512.inl index 66e83096104..b70a7691e2b 100644 --- a/src/gallium/drivers/swr/rasterizer/common/simdlib_128_avx512.inl +++ b/src/gallium/drivers/swr/rasterizer/common/simdlib_128_avx512.inl @@ -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, diff --git a/src/gallium/drivers/swr/rasterizer/common/simdlib_256_avx512.inl b/src/gallium/drivers/swr/rasterizer/common/simdlib_256_avx512.inl index 3f93cfbd7f1..3fcfd250f91 100644 --- a/src/gallium/drivers/swr/rasterizer/common/simdlib_256_avx512.inl +++ b/src/gallium/drivers/swr/rasterizer/common/simdlib_256_avx512.inl @@ -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, diff --git a/src/gallium/drivers/swr/rasterizer/common/simdlib_512_avx512.inl b/src/gallium/drivers/swr/rasterizer/common/simdlib_512_avx512.inl index c13b9f616aa..8de62f2a7e4 100644 --- a/src/gallium/drivers/swr/rasterizer/common/simdlib_512_avx512.inl +++ b/src/gallium/drivers/swr/rasterizer/common/simdlib_512_avx512.inl @@ -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); } |