fdo-mirrors/mesa
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/mesa/mesa.git synced 2026-05-05 00:58:05 +02:00
Code Issues Projects Releases Packages Wiki Activity Actions 2

swr/rast: make simd16 logicops avx512f safe

Browse source 
Express the simd16 logicops in terms of avx512f instructions.

Reviewed-by: Bruce Cherniak <bruce.cherniak@intel.com>
This commit is contained in:
Tim Rowley 2017-05-16 10:25:21 -05:00
parent 7be26a2d35
commit 2438932b7e
1 changed files with 10 additions and 4 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

14
src/gallium/drivers/swr/rasterizer/common/simd16intrin.h
View file

@ -941,10 +941,16 @@ INLINE simd16scalar SIMDAPI _simd16_cmp_ps_temp(simd16scalar a, simd16scalar b)
#define _simd16_castpd_ps _mm512_castpd_ps
#define _simd16_castps_pd _mm512_castps_pd
#define _simd16_and_ps _mm512_and_ps
#define _simd16_andnot_ps _mm512_andnot_ps
#define _simd16_or_ps _mm512_or_ps
#define _simd16_xor_ps _mm512_xor_ps
// _mm512_and_ps (and other bitwise operations) exist in AVX512DQ,
// while the functionally equivalent _mm512_and_epi32 is in AVX512F.
// Define the _simd16_*_ps versions in terms of AVX512F for broader
// support.
#define _simd16_logicop_ps(a, b, op) _simd16_castsi_ps(op##_epi32(_simd16_castps_si(a), _simd16_castps_si(b)))
#define _simd16_and_ps(a, b) _simd16_logicop_ps(a, b, _mm512_and)
#define _simd16_andnot_ps(a, b) _simd16_logicop_ps(a, b, _mm512_andnot)
#define _simd16_or_ps(a, b) _simd16_logicop_ps(a, b, _mm512_or)
#define _simd16_xor_ps(a, b) _simd16_logicop_ps(a, b, _mm512_xor)
template <int mode>
INLINE simd16scalar SIMDAPI _simd16_round_ps_temp(simd16scalar a)