diff options
| author | Kirill Yukhin <kirill.yukhin@intel.com> | 2014-07-19 09:44:34 +0000 |
|---|---|---|
| committer | Kirill Yukhin <kirill.yukhin@intel.com> | 2014-07-19 09:44:34 +0000 |
| commit | e8adc0d2aa94cd3fabb32687214e9aa3c6df84cd (patch) | |
| tree | e52ab4bdaab79d0b02ed31b25f44ff3cfba957b9 /gcc/testsuite/gcc.target/i386/avx512bw-vpcmpub-2.c | |
| parent | 614ec7014faca3ecc66e9f3f8cf7d0e37860d720 (diff) | |
Initial support for AVX-512{VL,BW,DQ}avx512-vlbwdq
git-svn-id: https://gcc.gnu.org/svn/gcc/branches/avx512-vlbwdq@212839 138bc75d-0d04-0410-961f-82ee72b054a4
Diffstat (limited to 'gcc/testsuite/gcc.target/i386/avx512bw-vpcmpub-2.c')
| -rw-r--r-- | gcc/testsuite/gcc.target/i386/avx512bw-vpcmpub-2.c | 107 |
1 files changed, 107 insertions, 0 deletions
diff --git a/gcc/testsuite/gcc.target/i386/avx512bw-vpcmpub-2.c b/gcc/testsuite/gcc.target/i386/avx512bw-vpcmpub-2.c new file mode 100644 index 00000000000..be288c9b3e6 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/avx512bw-vpcmpub-2.c @@ -0,0 +1,107 @@ +/* { dg-do run } */ +/* { dg-options "-O2 -mavx512bw -DAVX512BW" } */ +/* { dg-require-effective-target avx512bw } */ + +#include "avx512f-helper.h" + +#include <math.h> +#define SIZE (AVX512F_LEN / 16) +#include "avx512f-mask-type.h" + +#if AVX512F_LEN == 512 +#undef CMP +#define CMP(imm, rel) \ + dst_ref = 0; \ + for (i = 0; i < 64; i++) \ + { \ + dst_ref = ((rel) << i) | dst_ref; \ + } \ + source1.x = _mm512_loadu_si512 (s1); \ + source2.x = _mm512_loadu_si512 (s2); \ + dst1 = _mm512_cmp_epu8_mask (source1.x, source2.x, imm);\ + dst2 = _mm512_mask_cmp_epu8_mask (mask, source1.x, source2.x, imm);\ + if (dst_ref != dst1) abort(); \ + if ((mask & dst_ref) != dst2) abort(); +#endif + +#if AVX512F_LEN == 256 +#undef CMP +#define CMP(imm, rel) \ + dst_ref = 0; \ + for (i = 0; i < 32; i++) \ + { \ + dst_ref = ((rel) << i) | dst_ref; \ + } \ + source1.x = _mm256_loadu_si256 ((__m256i*)s1); \ + source2.x = _mm256_loadu_si256 ((__m256i*)s2); \ + dst1 = _mm256_cmp_epu8_mask (source1.x, source2.x, imm);\ + dst2 = _mm256_mask_cmp_epu8_mask (mask, source1.x, source2.x, imm);\ + if (dst_ref != dst1) abort(); \ + if ((mask & dst_ref) != dst2) abort(); +#endif + +#if AVX512F_LEN == 128 +#undef CMP +#define CMP(imm, rel) \ + dst_ref = 0; \ + for (i = 0; i < 16; i++) \ + { \ + dst_ref = ((rel) << i) | dst_ref; \ + } \ + source1.x = _mm_loadu_si128 ((__m128i*)s1); \ + source2.x = _mm_loadu_si128 ((__m128i*)s2); \ + dst1 = _mm_cmp_epu8_mask (source1.x, source2.x, imm);\ + dst2 = _mm_mask_cmp_epu8_mask (mask, source1.x, source2.x, imm);\ + if (dst_ref != dst1) abort(); \ + if ((mask & dst_ref) != dst2) abort(); +#endif + +void +TEST () +{ + unsigned char s1[64] = {34, 78, 53, 64, + 1, 57, 11, 231, + 14, 45, 71, 75, + 55, 66, 21, 73, + 34, 68, 3, 56, + 1, 57, 111, 241, + 14, 15, 61, 75, + 55, 16, 52, 3, + 34, 78, 53, 64, + 1, 57, 11, 231, + 14, 45, 71, 75, + 55, 66, 21, 73, + 34, 68, 3, 56, + 1, 57, 111, 241, + 14, 15, 61, 75, + 55, 16, 52, 3}; + unsigned char s2[64] = {4, 68, 86, 8, + 1, 46, 1, 1, + 45, 67, 36, 3, + 4, 39, 56, 56, + 124, 78, 53, 56, + 1, 46, 1, 12, + 45, 47, 36, 13, + 4, 35, 56, 67, + 4, 68, 86, 8, + 1, 46, 1, 1, + 45, 67, 36, 3, + 4, 39, 56, 56, + 124, 78, 53, 56, + 1, 46, 1, 12, + 45, 47, 36, 13, + 4, 35, 56, 67}; + UNION_TYPE (AVX512F_LEN, i_b) source1, source2; + MASK_TYPE dst1, dst2, dst_ref; + MASK_TYPE mask = MASK_VALUE; + int i; + + CMP(0x00, s1[i] == s2[i]); + CMP(0x01, s1[i] < s2[i]); + CMP(0x02, s1[i] <= s2[i]); + CMP(0x03, 0); + CMP(0x04, s1[i] != s2[i]); + CMP(0x05, s1[i] >= s2[i]); + CMP(0x06, s1[i] > s2[i]); + CMP(0x07, 1); +} |