AVX-512. 88/n. Add missed avx512bw/avx512vl cmp intrinsics.

gcc/
	* config/i386/avx512bwintrin.h: Add new intrinsics.
	* config/i386/avx512vlbwintrin.h: Ditto.
	* config/i386/avx512vlintrin.h: Ditto.
gcc/testsuite/
	* gcc.target/i386/avx512bw-vpcmpequb-1.c: New.
	* gcc.target/i386/avx512bw-vpcmpequb-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpequw-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpequw-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgeb-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgeb-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgeub-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgeub-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgeuw-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgeuw-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgew-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgew-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgtub-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgtub-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgtuw-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpgtuw-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpleb-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpleb-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpleub-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpleub-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpleuw-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpleuw-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmplew-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmplew-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpltb-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpltb-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpltub-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpltub-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpltuw-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpltuw-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpltw-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpltw-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpneqb-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpneqb-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpnequb-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpnequb-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpnequw-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpnequw-2.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpneqw-1.c: Ditto.
	* gcc.target/i386/avx512bw-vpcmpneqw-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpequb-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpequd-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpequd-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpequq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpequq-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpequw-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpged-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgeq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgeud-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgeuq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgtub-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgtud-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgtud-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgtuq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgtuq-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpgtuw-2.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpled-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpleq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpleud-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpleuq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpltd-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpltq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpltud-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpltuq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpneqd-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpneqq-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpnequd-1.c: Ditto.
	* gcc.target/i386/avx512vl-vpcmpnequq-1.c: Ditto.


git-svn-id: svn+ssh://gcc.gnu.org/svn/gcc/trunk@216819 138bc75d-0d04-0410-961f-82ee72b054a4

1 files changed, 21 insertions, 0 deletions

diff --git a/gcc/testsuite/gcc.target/i386/avx512vl-vpcmpneqq-1.c b/gcc/testsuite/gcc.target/i386/avx512vl-vpcmpneqq-1.c
new file mode 100644
index 00000000000..eeacd087ece
--- /dev/null
+++ b/gcc/testsuite/gcc.target/i386/avx512vl-vpcmpneqq-1.c
@@ -0,0 +1,21 @@
+/* { dg-do compile } */
+/* { dg-options "-mavx512vl -O2" } */
+/* { dg-final { scan-assembler "vpcmpq\[ \\t\]+\[^\n\]*%ymm\[0-9\]\[^\n\]*%k\[1-7\]\[^\{\]" } } */
+/* { dg-final { scan-assembler "vpcmpq\[ \\t\]+\[^\n\]*%xmm\[0-9\]\[^\n\]*%k\[1-7\]\[^\{\]" } } */
+/* { dg-final { scan-assembler "vpcmpq\[ \\t\]+\[^\n\]*%ymm\[0-9\]\[^\n\]*%k\[1-7\]\{%k\[1-7\]\}" } } */
+/* { dg-final { scan-assembler "vpcmpq\[ \\t\]+\[^\n\]*%xmm\[0-9\]\[^\n\]*%k\[1-7\]\{%k\[1-7\]\}" } } */
+
+#include <immintrin.h>
+
+volatile __m256i x256;
+volatile __m128i x128;
+volatile __mmask8 m;
+
+void extern
+avx512vl_test (void)
+{
+  m = _mm_cmpneq_epi64_mask (x128, x128);
+  m = _mm256_cmpneq_epi64_mask (x256, x256);
+  m = _mm_mask_cmpneq_epi64_mask (3, x128, x128);
+  m = _mm256_mask_cmpneq_epi64_mask (3, x256, x256);
+}