Skip to content

R
riscv-gcc-1
Commit 7e23f4a6 by Olga Makhotina Committed by Kirill Yukhin
Options

Adding missing CMP* intrinsics 

gcc/
	* config/i386/avx512fintrin.h (_mm512_cmpeq_pd_mask,
	_mm512_cmple_pd_mask, _mm512_cmplt_pd_mask,
	_mm512_cmpneq_pd_mask, _mm512_cmpnle_pd_mask,
	_mm512_cmpnlt_pd_mask, _mm512_cmpord_pd_mask,
	_mm512_cmpunord_pd_mask, _mm512_mask_cmpeq_pd_mask,
	_mm512_mask_cmple_pd_mask, _mm512_mask_cmplt_pd_mask,
	_mm512_mask_cmpneq_pd_mask, _mm512_mask_cmpnle_pd_mask,
	_mm512_mask_cmpnlt_pd_mask, _mm512_mask_cmpord_pd_mask,
	_mm512_mask_cmpunord_pd_mask, _mm512_cmpeq_ps_mask,
	_mm512_cmple_ps_mask, _mm512_cmplt_ps_mask,
	_mm512_cmpneq_ps_mask, _mm512_cmpnle_ps_mask,
	_mm512_cmpnlt_ps_mask, _mm512_cmpord_ps_mask,
	_mm512_cmpunord_ps_mask, _mm512_mask_cmpeq_ps_mask,
	_mm512_mask_cmple_ps_mask, _mm512_mask_cmplt_ps_mask,
	_mm512_mask_cmpneq_ps_mask, _mm512_mask_cmpnle_ps_mask,
	_mm512_mask_cmpnlt_ps_mask, _mm512_mask_cmpord_ps_mask,
	_mm512_mask_cmpunord_ps_mask): New intrinsics.
gcc/testsuite/
	* gcc.target/i386/avx512f-vcmpps-1.c (_mm512_cmpeq_ps_mask,
	_mm512_cmple_ps_mask, _mm512_cmplt_ps_mask,
	_mm512_cmpneq_ps_mask, _mm512_cmpnle_ps_mask,
	_mm512_cmpnlt_ps_mask, _mm512_cmpord_ps_mask,
	_mm512_cmpunord_ps_mask, _mm512_mask_cmpeq_ps_mask,
	_mm512_mask_cmple_ps_mask, _mm512_mask_cmplt_ps_mask,
	_mm512_mask_cmpneq_ps_mask, _mm512_mask_cmpnle_ps_mask,
	_mm512_mask_cmpnlt_ps_mask, _mm512_mask_cmpord_ps_mask,
	_mm512_mask_cmpunord_ps_mask): Test new intrinsics.
	* gcc.target/i386/avx512f-vcmpps-2.c (_mm512_cmpeq_ps_mask,
	_mm512_cmple_ps_mask, _mm512_cmplt_ps_mask,
	_mm512_cmpneq_ps_mask, _mm512_cmpnle_ps_mask,
	_mm512_cmpnlt_ps_mask, _mm512_cmpord_ps_mask,
	_mm512_cmpunord_ps_mask, _mm512_mask_cmpeq_ps_mask,
	_mm512_mask_cmple_ps_mask, _mm512_mask_cmplt_ps_mask,
	_mm512_mask_cmpneq_ps_mask, _mm512_mask_cmpnle_ps_mask,
	_mm512_mask_cmpnlt_ps_mask, _mm512_mask_cmpord_ps_mask,
	_mm512_mask_cmpunord_ps_mask): Test new intrinsics.
	* gcc.target/i386/avx512f-vcmppd-1.c (_mm512_cmpeq_pd_mask,
	_mm512_cmple_pd_mask, _mm512_cmplt_pd_mask,
	_mm512_cmpneq_pd_mask, _mm512_cmpnle_pd_mask,
	_mm512_cmpnlt_pd_mask, _mm512_cmpord_pd_mask,
	_mm512_cmpunord_pd_mask, _mm512_mask_cmpeq_pd_mask,
	_mm512_mask_cmple_pd_mask, _mm512_mask_cmplt_pd_mask,
	_mm512_mask_cmpneq_pd_mask, _mm512_mask_cmpnle_pd_mask,
	_mm512_mask_cmpnlt_pd_mask, _mm512_mask_cmpord_pd_mask,
	_mm512_mask_cmpunord_pd_mask): Test new intrinsics.
	* gcc.target/i386/avx512f-vcmppd-2.c (_mm512_cmpeq_pd_mask,
	_mm512_cmple_pd_mask, _mm512_cmplt_pd_mask,
	_mm512_cmpneq_pd_mask, _mm512_cmpnle_pd_mask,
	_mm512_cmpnlt_pd_mask, _mm512_cmpord_pd_mask,
	_mm512_cmpunord_pd_mask, _mm512_mask_cmpeq_pd_mask,
	_mm512_mask_cmple_pd_mask, _mm512_mask_cmplt_pd_mask,
	_mm512_mask_cmpneq_pd_mask, _mm512_mask_cmpnle_pd_mask,
	_mm512_mask_cmpnlt_pd_mask, _mm512_mask_cmpord_pd_mask,
	_mm512_mask_cmpunord_pd_mask): Test new intrinsics.

From-SVN: r254118
parent 73b0ac0b
Showing with 200 additions and 71 deletions
gcc/ChangeLog
2017-10-26 Olga Makhotina <olga.makhotina@intel.com>
* config/i386/avx512fintrin.h (_mm512_cmpeq_pd_mask,
_mm512_cmple_pd_mask, _mm512_cmplt_pd_mask,
_mm512_cmpneq_pd_mask, _mm512_cmpnle_pd_mask,
_mm512_cmpnlt_pd_mask, _mm512_cmpord_pd_mask,
_mm512_cmpunord_pd_mask, _mm512_mask_cmpeq_pd_mask,
_mm512_mask_cmple_pd_mask, _mm512_mask_cmplt_pd_mask,
_mm512_mask_cmpneq_pd_mask, _mm512_mask_cmpnle_pd_mask,
_mm512_mask_cmpnlt_pd_mask, _mm512_mask_cmpord_pd_mask,
_mm512_mask_cmpunord_pd_mask, _mm512_cmpeq_ps_mask,
_mm512_cmple_ps_mask, _mm512_cmplt_ps_mask,
_mm512_cmpneq_ps_mask, _mm512_cmpnle_ps_mask,
_mm512_cmpnlt_ps_mask, _mm512_cmpord_ps_mask,
_mm512_cmpunord_ps_mask, _mm512_mask_cmpeq_ps_mask,
_mm512_mask_cmple_ps_mask, _mm512_mask_cmplt_ps_mask,
_mm512_mask_cmpneq_ps_mask, _mm512_mask_cmpnle_ps_mask,
_mm512_mask_cmpnlt_ps_mask, _mm512_mask_cmpord_ps_mask,
_mm512_mask_cmpunord_ps_mask): New intrinsics.
2017-10-26 Michael Meissner <meissner@linux.vnet.ibm.com> 2017-10-26 Michael Meissner <meissner@linux.vnet.ibm.com>
* config/rs6000/aix.h (TARGET_IEEEQUAD_DEFAULT): Set long double * config/rs6000/aix.h (TARGET_IEEEQUAD_DEFAULT): Set long double
gcc/testsuite/ChangeLog
2017-10-26 Olga Makhotina <olga.makhotina@intel.com>
* gcc.target/i386/avx512f-vcmpps-1.c (_mm512_cmpeq_ps_mask,
_mm512_cmple_ps_mask, _mm512_cmplt_ps_mask,
_mm512_cmpneq_ps_mask, _mm512_cmpnle_ps_mask,
_mm512_cmpnlt_ps_mask, _mm512_cmpord_ps_mask,
_mm512_cmpunord_ps_mask, _mm512_mask_cmpeq_ps_mask,
_mm512_mask_cmple_ps_mask, _mm512_mask_cmplt_ps_mask,
_mm512_mask_cmpneq_ps_mask, _mm512_mask_cmpnle_ps_mask,
_mm512_mask_cmpnlt_ps_mask, _mm512_mask_cmpord_ps_mask,
_mm512_mask_cmpunord_ps_mask): Test new intrinsics.
* gcc.target/i386/avx512f-vcmpps-2.c (_mm512_cmpeq_ps_mask,
_mm512_cmple_ps_mask, _mm512_cmplt_ps_mask,
_mm512_cmpneq_ps_mask, _mm512_cmpnle_ps_mask,
_mm512_cmpnlt_ps_mask, _mm512_cmpord_ps_mask,
_mm512_cmpunord_ps_mask, _mm512_mask_cmpeq_ps_mask,
_mm512_mask_cmple_ps_mask, _mm512_mask_cmplt_ps_mask,
_mm512_mask_cmpneq_ps_mask, _mm512_mask_cmpnle_ps_mask,
_mm512_mask_cmpnlt_ps_mask, _mm512_mask_cmpord_ps_mask,
_mm512_mask_cmpunord_ps_mask): Test new intrinsics.
* gcc.target/i386/avx512f-vcmppd-1.c (_mm512_cmpeq_pd_mask,
_mm512_cmple_pd_mask, _mm512_cmplt_pd_mask,
_mm512_cmpneq_pd_mask, _mm512_cmpnle_pd_mask,
_mm512_cmpnlt_pd_mask, _mm512_cmpord_pd_mask,
_mm512_cmpunord_pd_mask, _mm512_mask_cmpeq_pd_mask,
_mm512_mask_cmple_pd_mask, _mm512_mask_cmplt_pd_mask,
_mm512_mask_cmpneq_pd_mask, _mm512_mask_cmpnle_pd_mask,
_mm512_mask_cmpnlt_pd_mask, _mm512_mask_cmpord_pd_mask,
_mm512_mask_cmpunord_pd_mask): Test new intrinsics.
* gcc.target/i386/avx512f-vcmppd-2.c (_mm512_cmpeq_pd_mask,
_mm512_cmple_pd_mask, _mm512_cmplt_pd_mask,
_mm512_cmpneq_pd_mask, _mm512_cmpnle_pd_mask,
_mm512_cmpnlt_pd_mask, _mm512_cmpord_pd_mask,
_mm512_cmpunord_pd_mask, _mm512_mask_cmpeq_pd_mask,
_mm512_mask_cmple_pd_mask, _mm512_mask_cmplt_pd_mask,
_mm512_mask_cmpneq_pd_mask, _mm512_mask_cmpnle_pd_mask,
_mm512_mask_cmpnlt_pd_mask, _mm512_mask_cmpord_pd_mask,
_mm512_mask_cmpunord_pd_mask): Test new intrinsics.
2017-10-26 Wilco Dijkstra <wdijkstr@arm.com> 2017-10-26 Wilco Dijkstra <wdijkstr@arm.com>
* gcc.target/aarch64/ldp_stp_unaligned_2.c: New file. * gcc.target/aarch64/ldp_stp_unaligned_2.c: New file.
......
gcc/testsuite/gcc.target/i386/avx512f-vcmppd-1.c
/* { dg-do compile } */ /* { dg-do compile } */
/* { dg-options "-O2 -mavx512f" } */ /* { dg-options "-O2 -mavx512f" } */
/* { dg-final { scan-assembler-times "vcmppd\[ \\t\]+\[^\{\n\]*\[^\}\]%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\](?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcmppd\[ \\t\]+\[^\{\n\]*\[^\}\]%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\](?:\n|\[ \\t\]+#)" 9 } } */
/* { dg-final { scan-assembler-times "vcmppd\[ \\t\]+\[^\{\n\]*\[^\}\]%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\]\{%k\[0-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcmppd\[ \\t\]+\[^\{\n\]*\[^\}\]%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\]\{%k\[0-7\]\}(?:\n|\[ \\t\]+#)" 9 } } */
/* { dg-final { scan-assembler-times "vcmppd\[ \\t\]+\[^\{\n\]*\{sae\}\[^\n\]*%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\](?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcmppd\[ \\t\]+\[^\{\n\]*\{sae\}\[^\n\]*%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\](?:\n|\[ \\t\]+#)" 1 } } */
/* { dg-final { scan-assembler-times "vcmppd\[ \\t\]+\[^\{\n\]*\{sae\}\[^\n\]*%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\]\{%k\[0-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcmppd\[ \\t\]+\[^\{\n\]*\{sae\}\[^\n\]*%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\]\{%k\[0-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
...@@ -17,4 +17,29 @@ avx512f_test (void) ...@@ -17,4 +17,29 @@ avx512f_test (void)
m = _mm512_mask_cmp_pd_mask (m, x, x, _CMP_FALSE_OQ); m = _mm512_mask_cmp_pd_mask (m, x, x, _CMP_FALSE_OQ);
m = _mm512_cmp_round_pd_mask (x, x, _CMP_FALSE_OQ, _MM_FROUND_NO_EXC); m = _mm512_cmp_round_pd_mask (x, x, _CMP_FALSE_OQ, _MM_FROUND_NO_EXC);
m = _mm512_mask_cmp_round_pd_mask (m, x, x, _CMP_FALSE_OQ, _MM_FROUND_NO_EXC); m = _mm512_mask_cmp_round_pd_mask (m, x, x, _CMP_FALSE_OQ, _MM_FROUND_NO_EXC);
m = _mm512_cmpeq_pd_mask (x, x);
m = _mm512_mask_cmpeq_pd_mask (m, x, x);
m = _mm512_cmplt_pd_mask (x, x);
m = _mm512_mask_cmplt_pd_mask (m, x, x);
m = _mm512_cmple_pd_mask (x, x);
m = _mm512_mask_cmple_pd_mask (m, x, x);
m = _mm512_cmpunord_pd_mask (x, x);
m = _mm512_mask_cmpunord_pd_mask (m, x, x);
m = _mm512_cmpneq_pd_mask (x, x);
m = _mm512_mask_cmpneq_pd_mask (m, x, x);
m = _mm512_cmpnlt_pd_mask (x, x);
m = _mm512_mask_cmpnlt_pd_mask (m, x, x);
m = _mm512_cmpnle_pd_mask (x, x);
m = _mm512_mask_cmpnle_pd_mask (m, x, x);
m = _mm512_cmpord_pd_mask (x, x);
m = _mm512_mask_cmpord_pd_mask (m, x, x);
} }
gcc/testsuite/gcc.target/i386/avx512f-vcmppd-2.c
...@@ -11,58 +11,69 @@ ...@@ -11,58 +11,69 @@
#define SIZE (AVX512F_LEN / 64) #define SIZE (AVX512F_LEN / 64)
#include "avx512f-mask-type.h" #include "avx512f-mask-type.h"
#undef SUF
#undef SSIZE
#undef GEN_CMP
#undef CHECK_CMP
#if AVX512F_LEN == 512 #if AVX512F_LEN == 512
#define CMP(imm, rel) \ #define SUF(fun) _mm512##fun
dst_ref = 0; \ #define SSIZE 8
for (i = 0; i < 8; i++) \
{ \ #define GEN_CMP(type) \
dst_ref = (((int) rel) << i) | dst_ref; \ { \
} \ dst3 = _mm512_cmp##type##_pd_mask(source1.x, source2.x);\
source1.x = _mm512_loadu_pd(s1); \ dst4 = _mm512_mask_cmp##type##_pd_mask(mask, source1.x, source2.x);\
source2.x = _mm512_loadu_pd(s2); \ if (dst3 != dst1) abort(); \
dst1 = _mm512_cmp_pd_mask(source1.x, source2.x, imm);\ if (dst4 != dst2) abort(); \
dst2 = _mm512_mask_cmp_pd_mask(mask, source1.x, source2.x, imm);\ }
if (dst_ref != dst1) abort(); \
if ((dst_ref & mask) != dst2) abort(); #define CHECK_CMP(imm) \
if (imm == _CMP_EQ_OQ) GEN_CMP(eq) \
if (imm == _CMP_LT_OS) GEN_CMP(lt) \
if (imm == _CMP_LE_OS) GEN_CMP(le) \
if (imm == _CMP_UNORD_Q) GEN_CMP(unord) \
if (imm == _CMP_NEQ_UQ) GEN_CMP(neq) \
if (imm == _CMP_NLT_US) GEN_CMP(nlt) \
if (imm == _CMP_NLE_US) GEN_CMP(nle) \
if (imm == _CMP_ORD_Q) GEN_CMP(ord)
#endif #endif
#if AVX512F_LEN == 256 #if AVX512F_LEN == 256
#undef CMP #define SUF(fun) _mm256##fun
#define CMP(imm, rel) \ #define SSIZE 4
dst_ref = 0; \ #define GEN_CMP(type)
for (i = 0; i < 4; i++) \ #define CHECK_CMP(imm)
{ \
dst_ref = (((int) rel) << i) | dst_ref; \
} \
source1.x = _mm256_loadu_pd(s1); \
source2.x = _mm256_loadu_pd(s2); \
dst1 = _mm256_cmp_pd_mask(source1.x, source2.x, imm);\
dst2 = _mm256_mask_cmp_pd_mask(mask, source1.x, source2.x, imm);\
if (dst_ref != dst1) abort(); \
if ((dst_ref & mask) != dst2) abort();
#endif #endif
#if AVX512F_LEN == 128 #if AVX512F_LEN == 128
#define SUF(fun) _mm##fun
#define SSIZE 2
#define GEN_CMP(type)
#define CHECK_CMP(imm)
#endif
#undef CMP #undef CMP
#define CMP(imm, rel) \ #define CMP(imm, rel) \
dst_ref = 0; \ dst_ref = 0; \
for (i = 0; i < 2; i++) \ for (i = 0; i < SSIZE; i++) \
{ \ { \
dst_ref = (((int) rel) << i) | dst_ref; \ dst_ref = (((int) rel) << i) | dst_ref; \
} \ } \
source1.x = _mm_loadu_pd(s1); \ source1.x = SUF(_loadu_pd)(s1); \
source2.x = _mm_loadu_pd(s2); \ source2.x = SUF(_loadu_pd)(s2); \
dst1 = _mm_cmp_pd_mask(source1.x, source2.x, imm);\ dst1 = SUF(_cmp_pd_mask)(source1.x, source2.x, imm);\
dst2 = _mm_mask_cmp_pd_mask(mask, source1.x, source2.x, imm);\ dst2 = SUF(_mask_cmp_pd_mask)(mask, source1.x, source2.x, imm);\
if (dst_ref != dst1) abort(); \ if (dst_ref != dst1) abort(); \
if ((dst_ref & mask) != dst2) abort(); if ((dst_ref & mask) != dst2) abort(); \
#endif CHECK_CMP(imm)
void void
TEST () TEST ()
{ {
UNION_TYPE (AVX512F_LEN, d) source1, source2; UNION_TYPE (AVX512F_LEN, d) source1, source2;
MASK_TYPE dst1, dst2, dst_ref; MASK_TYPE dst1, dst2, dst3, dst4, dst_ref;
MASK_TYPE mask = MASK_VALUE; MASK_TYPE mask = MASK_VALUE;
int i; int i;
double s1[8]={2134.3343, 6678.346, 453.345635, 54646.464, double s1[8]={2134.3343, 6678.346, 453.345635, 54646.464,
......
gcc/testsuite/gcc.target/i386/avx512f-vcmpps-1.c
/* { dg-do compile } */ /* { dg-do compile } */
/* { dg-options "-O2 -mavx512f" } */ /* { dg-options "-O2 -mavx512f" } */
/* { dg-final { scan-assembler-times "vcmpps\[ \\t\]+\[^\{\n\]*\[^\}\]%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\](?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcmpps\[ \\t\]+\[^\{\n\]*\[^\}\]%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\](?:\n|\[ \\t\]+#)" 9 } } */
/* { dg-final { scan-assembler-times "vcmpps\[ \\t\]+\[^\{\n\]*\[^\}\]%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\]\{%k\[0-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcmpps\[ \\t\]+\[^\{\n\]*\[^\}\]%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\]\{%k\[0-7\]\}(?:\n|\[ \\t\]+#)" 9 } } */
/* { dg-final { scan-assembler-times "vcmpps\[ \\t\]+\[^\{\n\]*\{sae\}\[^\n\]*%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\](?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcmpps\[ \\t\]+\[^\{\n\]*\{sae\}\[^\n\]*%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\](?:\n|\[ \\t\]+#)" 1 } } */
/* { dg-final { scan-assembler-times "vcmpps\[ \\t\]+\[^\{\n\]*\{sae\}\[^\n\]*%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\]\{%k\[0-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcmpps\[ \\t\]+\[^\{\n\]*\{sae\}\[^\n\]*%zmm\[0-9\]+\[^\n^k\]*%k\[1-7\]\{%k\[0-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */
...@@ -17,4 +17,28 @@ avx512f_test (void) ...@@ -17,4 +17,28 @@ avx512f_test (void)
m = _mm512_mask_cmp_ps_mask (m, x, x, _CMP_FALSE_OQ); m = _mm512_mask_cmp_ps_mask (m, x, x, _CMP_FALSE_OQ);
m = _mm512_cmp_round_ps_mask (x, x, _CMP_FALSE_OQ, _MM_FROUND_NO_EXC); m = _mm512_cmp_round_ps_mask (x, x, _CMP_FALSE_OQ, _MM_FROUND_NO_EXC);
m = _mm512_mask_cmp_round_ps_mask (m, x, x, _CMP_FALSE_OQ, _MM_FROUND_NO_EXC); m = _mm512_mask_cmp_round_ps_mask (m, x, x, _CMP_FALSE_OQ, _MM_FROUND_NO_EXC);
m = _mm512_cmpeq_ps_mask (x, x);
m = _mm512_mask_cmpeq_ps_mask (m, x, x);
m = _mm512_cmplt_ps_mask (x, x);
m = _mm512_mask_cmplt_ps_mask (m, x, x);
m = _mm512_cmple_ps_mask (x, x);
m = _mm512_mask_cmple_ps_mask (m, x, x);
m = _mm512_cmpunord_ps_mask (x, x);
m = _mm512_mask_cmpunord_ps_mask (m, x, x);
m = _mm512_cmpneq_ps_mask (x, x);
m = _mm512_mask_cmpneq_ps_mask (m, x, x);
m = _mm512_cmpnlt_ps_mask (x, x);
m = _mm512_mask_cmpnlt_ps_mask (m, x, x);
m = _mm512_cmpnle_ps_mask (x, x);
m = _mm512_mask_cmpnle_ps_mask (m, x, x);
m = _mm512_cmpord_ps_mask (x, x);
m = _mm512_mask_cmpord_ps_mask (m, x, x);
} }
gcc/testsuite/gcc.target/i386/avx512f-vcmpps-2.c
...@@ -11,59 +11,69 @@ ...@@ -11,59 +11,69 @@
#define SIZE (AVX512F_LEN / 32) #define SIZE (AVX512F_LEN / 32)
#include "avx512f-mask-type.h" #include "avx512f-mask-type.h"
#undef SUF
#undef SSIZE
#undef GEN_CMP
#undef CHECK_CMP
#if AVX512F_LEN == 512 #if AVX512F_LEN == 512
#undef CMP #define SUF(fun) _mm512##fun
#define CMP(imm, rel) \ #define SSIZE 16
dst_ref = 0; \
for (i = 0; i < 16; i++) \ #define GEN_CMP(type) \
{ \ { \
dst_ref = (((int) rel) << i) | dst_ref; \ dst3 = _mm512_cmp##type##_ps_mask(source1.x, source2.x);\
} \ dst4 = _mm512_mask_cmp##type##_ps_mask(mask, source1.x, source2.x);\
source1.x = _mm512_loadu_ps(s1); \ if (dst3 != dst1) abort(); \
source2.x = _mm512_loadu_ps(s2); \ if (dst4 != dst2) abort(); \
dst1 = _mm512_cmp_ps_mask(source1.x, source2.x, imm);\ }
dst2 = _mm512_mask_cmp_ps_mask(mask, source1.x, source2.x, imm);\
if (dst_ref != dst1) abort(); \ #define CHECK_CMP(imm) \
if ((dst_ref & mask) != dst2) abort(); if (imm == _CMP_EQ_OQ) GEN_CMP(eq) \
if (imm == _CMP_LT_OS) GEN_CMP(lt) \
if (imm == _CMP_LE_OS) GEN_CMP(le) \
if (imm == _CMP_UNORD_Q) GEN_CMP(unord) \
if (imm == _CMP_NEQ_UQ) GEN_CMP(neq) \
if (imm == _CMP_NLT_US) GEN_CMP(nlt) \
if (imm == _CMP_NLE_US) GEN_CMP(nle) \
if (imm == _CMP_ORD_Q) GEN_CMP(ord)
#endif #endif
#if AVX512F_LEN == 256 #if AVX512F_LEN == 256
#undef CMP #define SUF(fun) _mm256##fun
#define CMP(imm, rel) \ #define SSIZE 8
dst_ref = 0; \ #define GEN_CMP(type)
for (i = 0; i < 8; i++) \ #define CHECK_CMP(imm)
{ \
dst_ref = (((int) rel) << i) | dst_ref; \
} \
source1.x = _mm256_loadu_ps(s1); \
source2.x = _mm256_loadu_ps(s2); \
dst1 = _mm256_cmp_ps_mask(source1.x, source2.x, imm);\
dst2 = _mm256_mask_cmp_ps_mask(mask, source1.x, source2.x, imm);\
if (dst_ref != dst1) abort(); \
if ((dst_ref & mask) != dst2) abort();
#endif #endif
#if AVX512F_LEN == 128 #if AVX512F_LEN == 128
#define SUF(fun) _mm##fun
#define SSIZE 4
#define GEN_CMP(type)
#define CHECK_CMP(imm)
#endif
#undef CMP #undef CMP
#define CMP(imm, rel) \ #define CMP(imm, rel) \
dst_ref = 0; \ dst_ref = 0; \
for (i = 0; i < 4; i++) \ for (i = 0; i < SSIZE; i++) \
{ \ { \
dst_ref = (((int) rel) << i) | dst_ref; \ dst_ref = (((int) rel) << i) | dst_ref; \
} \ } \
source1.x = _mm_loadu_ps(s1); \ source1.x = SUF(_loadu_ps)(s1); \
source2.x = _mm_loadu_ps(s2); \ source2.x = SUF(_loadu_ps)(s2); \
dst1 = _mm_cmp_ps_mask(source1.x, source2.x, imm);\ dst1 = SUF(_cmp_ps_mask)(source1.x, source2.x, imm);\
dst2 = _mm_mask_cmp_ps_mask(mask, source1.x, source2.x, imm);\ dst2 = SUF(_mask_cmp_ps_mask)(mask, source1.x, source2.x, imm);\
if (dst_ref != dst1) abort(); \ if (dst_ref != dst1) abort(); \
if ((dst_ref & mask) != dst2) abort(); if ((dst_ref & mask) != dst2) abort(); \
#endif CHECK_CMP(imm)
void void
TEST () TEST ()
{ {
UNION_TYPE (AVX512F_LEN,) source1, source2; UNION_TYPE (AVX512F_LEN,) source1, source2;
MASK_TYPE dst1, dst2, dst_ref; MASK_TYPE dst1, dst2, dst3, dst4, dst_ref;
MASK_TYPE mask = MASK_VALUE; MASK_TYPE mask = MASK_VALUE;
int i; int i;
float s1[16] = {2134.3343, 6678.346, 453.345635, 54646.464, float s1[16] = {2134.3343, 6678.346, 453.345635, 54646.464,
......
Markdown is supported
0% or
You are about to add 0 people to the discussion. Proceed with caution.
Finish editing this message first!
Please register or to comment