predicates.md (const1256_operand): Remove.

gcc/
	* common/config/i386/predicates.md (const1256_operand): Remove.
	(const2356_operand): New.
	(const_1_to_2_operand): Remove.
	* config/i386/sse.md (avx512pf_gatherpf<mode>sf): Change hint value.
	(*avx512pf_gatherpf<mode>sf_mask): Ditto.
	(*avx512pf_gatherpf<mode>sf): Ditto.
	(avx512pf_gatherpf<mode>df): Ditto.
	(*avx512pf_gatherpf<mode>df_mask): Ditto.
	(*avx512pf_gatherpf<mode>df): Ditto.
	(avx512pf_scatterpf<mode>sf): Ditto.
	(*avx512pf_scatterpf<mode>sf_mask): Ditto.
	(*avx512pf_scatterpf<mode>sf): Ditto.
	(avx512pf_scatterpf<mode>df): Ditto.
	(*avx512pf_scatterpf<mode>df_mask): Ditto.
	(*avx512pf_scatterpf<mode>df): Ditto.
	* common/config/i386/xmmintrin.h (_mm_hint): Add _MM_HINT_ET0.

gcc/testsuite/
	* common/config/i386/predicates.md (const1256_operand): Remove.
	(const2356_operand): New.
	(const_1_to_2_operand): Remove.
	* config/i386/sse.md (avx512pf_gatherpf<mode>sf): Change hint value.
	(*avx512pf_gatherpf<mode>sf_mask): Ditto.
	(*avx512pf_gatherpf<mode>sf): Ditto.
	(avx512pf_gatherpf<mode>df): Ditto.
	(*avx512pf_gatherpf<mode>df_mask): Ditto.
	(*avx512pf_gatherpf<mode>df): Ditto.
	(avx512pf_scatterpf<mode>sf): Ditto.
	(*avx512pf_scatterpf<mode>sf_mask): Ditto.
	(*avx512pf_scatterpf<mode>sf): Ditto.
	(avx512pf_scatterpf<mode>df): Ditto.
	(*avx512pf_scatterpf<mode>df_mask): Ditto.
	(*avx512pf_scatterpf<mode>df): Ditto.
	* common/config/i386/xmmintrin.h (_mm_hint): Add _MM_HINT_ET0.

From-SVN: r208169

diff --git a/gcc/ChangeLog b/gcc/ChangeLog
index 3974f9c2d29e41de726e3143a8e47c8ec7fb61af..1f5bd62a6bcfd2dd02314783c2a97c542cb6eb95 100644 (file)
--- a/gcc/ChangeLog
+++ b/gcc/ChangeLog
@@ -1,3 +1,22 @@
+2014-02-25  Ilya Tocar  <ilya.tocar@intel.com>
+
+       * common/config/i386/predicates.md (const1256_operand): Remove.
+       (const2356_operand): New.
+       (const_1_to_2_operand): Remove.
+       * config/i386/sse.md (avx512pf_gatherpf<mode>sf): Change hint value.
+       (*avx512pf_gatherpf<mode>sf_mask): Ditto.
+       (*avx512pf_gatherpf<mode>sf): Ditto.
+       (avx512pf_gatherpf<mode>df): Ditto.
+       (*avx512pf_gatherpf<mode>df_mask): Ditto.
+       (*avx512pf_gatherpf<mode>df): Ditto.
+       (avx512pf_scatterpf<mode>sf): Ditto.
+       (*avx512pf_scatterpf<mode>sf_mask): Ditto.
+       (*avx512pf_scatterpf<mode>sf): Ditto.
+       (avx512pf_scatterpf<mode>df): Ditto.
+       (*avx512pf_scatterpf<mode>df_mask): Ditto.
+       (*avx512pf_scatterpf<mode>df): Ditto.
+       * common/config/i386/xmmintrin.h (_mm_hint): Add _MM_HINT_ET0.
+
 2014-02-26  Ilya Tocar  <ilya.tocar@intel.com>
 
        * config/i386/avx512fintrin.h (_mm512_testn_epi32_mask),

diff --git a/gcc/config/i386/predicates.md b/gcc/config/i386/predicates.md
index 3f53e2d1d41f2ee97daa214b042734bbdf0a99c7..70418f430227cbe710e4a8720dd39cd6970981f3 100644 (file)
--- a/gcc/config/i386/predicates.md
+++ b/gcc/config/i386/predicates.md
@@ -660,12 +660,12 @@
   return i == 2 || i == 4 || i == 8;
 })
 
-;; Match 1, 2, 5, or 6
-(define_predicate "const1256_operand"
+;; Match 2, 3, 5, or 6
+(define_predicate "const2356_operand"
   (match_code "const_int")
 {
   HOST_WIDE_INT i = INTVAL (op);
-  return i == 1 || i == 2 || i == 5 || i == 6;
+  return i == 2 || i == 3 || i == 5 || i == 6;
 })
 
 ;; Match 1, 2, 4, or 8
@@ -754,11 +754,6 @@
   return val <= 255*8 && val % 8 == 0;
 })
 
-;; Match 1 to 2.
-(define_predicate "const_1_to_2_operand"
-  (and (match_code "const_int")
-       (match_test "IN_RANGE (INTVAL (op), 1, 2)")))
-
 ;; Return true if OP is CONST_INT >= 1 and <= 31 (a valid operand
 ;; for shift & compare patterns, as shifting by 0 does not change flags).
 (define_predicate "const_1_to_31_operand"

diff --git a/gcc/config/i386/sse.md b/gcc/config/i386/sse.md
index f6de5d5de52032702e621fd70127c52e3ec8c384..5775bc67c1e208bbb3c069fc9bd920732df0a94f 100644 (file)
--- a/gcc/config/i386/sse.md
+++ b/gcc/config/i386/sse.md
@@ -12508,7 +12508,7 @@
          [(match_operand 2 "vsib_address_operand")
           (match_operand:VI48_512 1 "register_operand")
           (match_operand:SI 3 "const1248_operand")]))
-      (match_operand:SI 4 "const_1_to_2_operand")]
+      (match_operand:SI 4 "const_2_to_3_operand")]
      UNSPEC_GATHER_PREFETCH)]
   "TARGET_AVX512PF"
 {
@@ -12526,13 +12526,13 @@
            (match_operand:VI48_512 1 "register_operand" "v")
            (match_operand:SI 3 "const1248_operand" "n")]
           UNSPEC_VSIBADDR)])
-      (match_operand:SI 4 "const_1_to_2_operand" "n")]
+      (match_operand:SI 4 "const_2_to_3_operand" "n")]
      UNSPEC_GATHER_PREFETCH)]
   "TARGET_AVX512PF"
 {
   switch (INTVAL (operands[4]))
     {
-    case 1:
+    case 3:
       return "vgatherpf0<ssemodesuffix>ps\t{%5%{%0%}|%5%{%0%}}";
     case 2:
       return "vgatherpf1<ssemodesuffix>ps\t{%5%{%0%}|%5%{%0%}}";
@@ -12553,13 +12553,13 @@
            (match_operand:VI48_512 0 "register_operand" "v")
            (match_operand:SI 2 "const1248_operand" "n")]
           UNSPEC_VSIBADDR)])
-      (match_operand:SI 3 "const_1_to_2_operand" "n")]
+      (match_operand:SI 3 "const_2_to_3_operand" "n")]
      UNSPEC_GATHER_PREFETCH)]
   "TARGET_AVX512PF"
 {
   switch (INTVAL (operands[3]))
     {
-    case 1:
+    case 3:
       return "vgatherpf0<ssemodesuffix>ps\t{%4|%4}";
     case 2:
       return "vgatherpf1<ssemodesuffix>ps\t{%4|%4}";
@@ -12580,7 +12580,7 @@
          [(match_operand 2 "vsib_address_operand")
           (match_operand:VI4_256_8_512 1 "register_operand")
           (match_operand:SI 3 "const1248_operand")]))
-      (match_operand:SI 4 "const_1_to_2_operand")]
+      (match_operand:SI 4 "const_2_to_3_operand")]
      UNSPEC_GATHER_PREFETCH)]
   "TARGET_AVX512PF"
 {
@@ -12598,13 +12598,13 @@
            (match_operand:VI4_256_8_512 1 "register_operand" "v")
            (match_operand:SI 3 "const1248_operand" "n")]
           UNSPEC_VSIBADDR)])
-      (match_operand:SI 4 "const_1_to_2_operand" "n")]
+      (match_operand:SI 4 "const_2_to_3_operand" "n")]
      UNSPEC_GATHER_PREFETCH)]
   "TARGET_AVX512PF"
 {
   switch (INTVAL (operands[4]))
     {
-    case 1:
+    case 3:
       return "vgatherpf0<ssemodesuffix>pd\t{%5%{%0%}|%5%{%0%}}";
     case 2:
       return "vgatherpf1<ssemodesuffix>pd\t{%5%{%0%}|%5%{%0%}}";
@@ -12625,13 +12625,13 @@
            (match_operand:VI4_256_8_512 0 "register_operand" "v")
            (match_operand:SI 2 "const1248_operand" "n")]
           UNSPEC_VSIBADDR)])
-      (match_operand:SI 3 "const_1_to_2_operand" "n")]
+      (match_operand:SI 3 "const_2_to_3_operand" "n")]
      UNSPEC_GATHER_PREFETCH)]
   "TARGET_AVX512PF"
 {
   switch (INTVAL (operands[3]))
     {
-    case 1:
+    case 3:
       return "vgatherpf0<ssemodesuffix>pd\t{%4|%4}";
     case 2:
       return "vgatherpf1<ssemodesuffix>pd\t{%4|%4}";
@@ -12652,7 +12652,7 @@
          [(match_operand 2 "vsib_address_operand")
           (match_operand:VI48_512 1 "register_operand")
           (match_operand:SI 3 "const1248_operand")]))
-      (match_operand:SI 4 "const1256_operand")]
+      (match_operand:SI 4 "const2356_operand")]
      UNSPEC_SCATTER_PREFETCH)]
   "TARGET_AVX512PF"
 {
@@ -12670,13 +12670,13 @@
            (match_operand:VI48_512 1 "register_operand" "v")
            (match_operand:SI 3 "const1248_operand" "n")]
           UNSPEC_VSIBADDR)])
-      (match_operand:SI 4 "const1256_operand" "n")]
+      (match_operand:SI 4 "const2356_operand" "n")]
      UNSPEC_SCATTER_PREFETCH)]
   "TARGET_AVX512PF"
 {
   switch (INTVAL (operands[4]))
     {
-    case 1:
+    case 3:
     case 5:
       return "vscatterpf0<ssemodesuffix>ps\t{%5%{%0%}|%5%{%0%}}";
     case 2:
@@ -12699,13 +12699,13 @@
            (match_operand:VI48_512 0 "register_operand" "v")
            (match_operand:SI 2 "const1248_operand" "n")]
           UNSPEC_VSIBADDR)])
-      (match_operand:SI 3 "const1256_operand" "n")]
+      (match_operand:SI 3 "const2356_operand" "n")]
      UNSPEC_SCATTER_PREFETCH)]
   "TARGET_AVX512PF"
 {
   switch (INTVAL (operands[3]))
     {
-    case 1:
+    case 3:
     case 5:
       return "vscatterpf0<ssemodesuffix>ps\t{%4|%4}";
     case 2:
@@ -12728,7 +12728,7 @@
          [(match_operand 2 "vsib_address_operand")
           (match_operand:VI4_256_8_512 1 "register_operand")
           (match_operand:SI 3 "const1248_operand")]))
-      (match_operand:SI 4 "const1256_operand")]
+      (match_operand:SI 4 "const2356_operand")]
      UNSPEC_SCATTER_PREFETCH)]
   "TARGET_AVX512PF"
 {
@@ -12746,13 +12746,13 @@
            (match_operand:VI4_256_8_512 1 "register_operand" "v")
            (match_operand:SI 3 "const1248_operand" "n")]
           UNSPEC_VSIBADDR)])
-      (match_operand:SI 4 "const1256_operand" "n")]
+      (match_operand:SI 4 "const2356_operand" "n")]
      UNSPEC_SCATTER_PREFETCH)]
   "TARGET_AVX512PF"
 {
   switch (INTVAL (operands[4]))
     {
-    case 1:
+    case 3:
     case 5:
       return "vscatterpf0<ssemodesuffix>pd\t{%5%{%0%}|%5%{%0%}}";
     case 2:
@@ -12775,13 +12775,13 @@
            (match_operand:VI4_256_8_512 0 "register_operand" "v")
            (match_operand:SI 2 "const1248_operand" "n")]
           UNSPEC_VSIBADDR)])
-      (match_operand:SI 3 "const1256_operand" "n")]
+      (match_operand:SI 3 "const2356_operand" "n")]
      UNSPEC_SCATTER_PREFETCH)]
   "TARGET_AVX512PF"
 {
   switch (INTVAL (operands[3]))
     {
-    case 1:
+    case 3:
     case 5:
       return "vscatterpf0<ssemodesuffix>pd\t{%4|%4}";
     case 2:

diff --git a/gcc/config/i386/xmmintrin.h b/gcc/config/i386/xmmintrin.h
index 9cefa2c50f7100ab331dad9b34ec12beaa66bd82..5967d7ed1e61f0511bfac984f6891e3abf1c16c3 100644 (file)
--- a/gcc/config/i386/xmmintrin.h
+++ b/gcc/config/i386/xmmintrin.h
@@ -54,6 +54,7 @@ typedef float __v4sf __attribute__ ((__vector_size__ (16)));
 enum _mm_hint
 {
   /* _MM_HINT_ET is _MM_HINT_T with set 3rd bit.  */
+  _MM_HINT_ET0 = 5,
   _MM_HINT_ET1 = 6,
   _MM_HINT_T0 = 3,
   _MM_HINT_T1 = 2,

diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog
index 124f5c716a0c9533824a5b5c2038addfac1d3ef0..48e2a1791fe8647915208d44b1a3656d761ec478 100644 (file)
--- a/gcc/testsuite/ChangeLog
+++ b/gcc/testsuite/ChangeLog
@@ -1,3 +1,22 @@
+2014-02-26  Ilya Tocar  <ilya.tocar@intel.com>
+
+       * common/config/i386/predicates.md (const1256_operand): Remove.
+       (const2356_operand): New.
+       (const_1_to_2_operand): Remove.
+       * config/i386/sse.md (avx512pf_gatherpf<mode>sf): Change hint value.
+       (*avx512pf_gatherpf<mode>sf_mask): Ditto.
+       (*avx512pf_gatherpf<mode>sf): Ditto.
+       (avx512pf_gatherpf<mode>df): Ditto.
+       (*avx512pf_gatherpf<mode>df_mask): Ditto.
+       (*avx512pf_gatherpf<mode>df): Ditto.
+       (avx512pf_scatterpf<mode>sf): Ditto.
+       (*avx512pf_scatterpf<mode>sf_mask): Ditto.
+       (*avx512pf_scatterpf<mode>sf): Ditto.
+       (avx512pf_scatterpf<mode>df): Ditto.
+       (*avx512pf_scatterpf<mode>df_mask): Ditto.
+       (*avx512pf_scatterpf<mode>df): Ditto.
+       * common/config/i386/xmmintrin.h (_mm_hint): Add _MM_HINT_ET0.
+
 2014-02-26  Ilya Tocar  <ilya.tocar@intel.com>
 
        * gcc.target/i386/avx512cd-vptestnmd-1.c: Change into ...

diff --git a/gcc/testsuite/gcc.target/i386/avx-1.c b/gcc/testsuite/gcc.target/i386/avx-1.c
index 12cfc68f912822d910865c3e4636f3a4819b2c0a..8f28921ca8634ca31a68268842146e03752194c6 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx-1.c
@@ -358,14 +358,14 @@
 #define __builtin_ia32_rsqrt28sd_round(A, B, C) __builtin_ia32_rsqrt28sd_round(A, B, 8)
 
 /* avx512pfintrin.h */
-#define __builtin_ia32_gatherpfdps(A, B, C, D, E) __builtin_ia32_gatherpfdps(A, B, C, 1, 1)
-#define __builtin_ia32_gatherpfqps(A, B, C, D, E) __builtin_ia32_gatherpfqps(A, B, C, 1, 1)
-#define __builtin_ia32_scatterpfdps(A, B, C, D, E) __builtin_ia32_scatterpfdps(A, B, C, 1, 1)
-#define __builtin_ia32_scatterpfqps(A, B, C, D, E) __builtin_ia32_scatterpfqps(A, B, C, 1, 1)
-#define __builtin_ia32_gatherpfdpd(A, B, C, D, E) __builtin_ia32_gatherpfdpd(A, B, C, 1, 1)
-#define __builtin_ia32_gatherpfqpd(A, B, C, D, E) __builtin_ia32_gatherpfqpd(A, B, C, 1, 1)
-#define __builtin_ia32_scatterpfdpd(A, B, C, D, E) __builtin_ia32_scatterpfdpd(A, B, C, 1, 1)
-#define __builtin_ia32_scatterpfqpd(A, B, C, D, E) __builtin_ia32_scatterpfqpd(A, B, C, 1, 1)
+#define __builtin_ia32_gatherpfdps(A, B, C, D, E) __builtin_ia32_gatherpfdps(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_gatherpfqps(A, B, C, D, E) __builtin_ia32_gatherpfqps(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_scatterpfdps(A, B, C, D, E) __builtin_ia32_scatterpfdps(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_scatterpfqps(A, B, C, D, E) __builtin_ia32_scatterpfqps(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_gatherpfdpd(A, B, C, D, E) __builtin_ia32_gatherpfdpd(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_gatherpfqpd(A, B, C, D, E) __builtin_ia32_gatherpfqpd(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_scatterpfdpd(A, B, C, D, E) __builtin_ia32_scatterpfdpd(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_scatterpfqpd(A, B, C, D, E) __builtin_ia32_scatterpfqpd(A, B, C, 1, _MM_HINT_T0)
 
 /* shaintrin.h */
 #define __builtin_ia32_sha1rnds4(A, B, C) __builtin_ia32_sha1rnds4(A, B, 1)

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0dpd-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0dpd-1.c
index fe366ee6c845134db3933211ac7771a2bfc03c3c..9051a1620e0cfa16f4e65d9f382bbb8f85ee7c8f 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0dpd-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0dpd-1.c
@@ -11,5 +11,5 @@ void *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_mask_prefetch_i32gather_pd (idx, m8, base, 8, 1);
+  _mm512_mask_prefetch_i32gather_pd (idx, m8, base, 8, _MM_HINT_T0);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0dps-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0dps-1.c
index df13cdbc71c72a1b7c684b85cdd9c2eea76e4073..bda31d77ba025498cfabac3d34b348aaf27b6ad9 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0dps-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0dps-1.c
@@ -11,5 +11,5 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_mask_prefetch_i32gather_ps (idx, m16, base, 8, 1);
+  _mm512_mask_prefetch_i32gather_ps (idx, m16, base, 8, _MM_HINT_T0);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0qpd-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0qpd-1.c
index ba7133521acd566864ce8dcb377d6e0ea84bf3fe..34bcecfe2dbc9942ecaafdacacad103c71ad8621 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0qpd-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0qpd-1.c
@@ -11,5 +11,5 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_mask_prefetch_i64gather_pd (idx, m8, base, 8, 1);
+  _mm512_mask_prefetch_i64gather_pd (idx, m8, base, 8, _MM_HINT_T0);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0qps-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0qps-1.c
index 945ac517cd55050f842ba17f31e89986e5f71a64..a9011b0814154a5e7bb60e49e7e366bc0f5dd691 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0qps-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf0qps-1.c
@@ -11,5 +11,5 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_mask_prefetch_i64gather_ps (idx, m8, base, 8, 1);
+  _mm512_mask_prefetch_i64gather_ps (idx, m8, base, 8, _MM_HINT_T0);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1dpd-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1dpd-1.c
index 5933376db06d12f640e0f4c51c839f600d0c72fa..a16f4d395e0dc320e109b1ab816e8f86aada00e6 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1dpd-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1dpd-1.c
@@ -11,5 +11,5 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_mask_prefetch_i32gather_pd (idx, m8, base, 8, 2);
+  _mm512_mask_prefetch_i32gather_pd (idx, m8, base, 8, _MM_HINT_T1);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1dps-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1dps-1.c
index da1046f8cf8d1bea125f7a06d24cc5fb52dd6508..c43152b01c9e802f398ef1de0cf3a285ae29e646 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1dps-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1dps-1.c
@@ -11,5 +11,5 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_mask_prefetch_i32gather_ps (idx, m16, base, 8, 2);
+  _mm512_mask_prefetch_i32gather_ps (idx, m16, base, 8, _MM_HINT_T1);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1qpd-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1qpd-1.c
index eb2c545d66985b2b4d8f8f35cb5d8c1431583104..ab9e351667a3105d7404731e8d09ee63efa4b421 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1qpd-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1qpd-1.c
@@ -11,5 +11,5 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_mask_prefetch_i64gather_pd (idx, m8, base, 8, 2);
+  _mm512_mask_prefetch_i64gather_pd (idx, m8, base, 8, _MM_HINT_T1);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1qps-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1qps-1.c
index 1c81836996a4ef8e087327140d8d79df2a466cbf..28d7cd666b19025bf6f61dd3eae7e0ef5a754e12 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1qps-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vgatherpf1qps-1.c
@@ -11,5 +11,5 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_mask_prefetch_i64gather_ps (idx, m8, base, 8, 2);
+  _mm512_mask_prefetch_i64gather_ps (idx, m8, base, 8, _MM_HINT_T1);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0dpd-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0dpd-1.c
index ff00bfa58d7bde3cc0e4bbfe14a964d56841c2eb..14d5c974498953a5426a9b5e21b7a453f30fc95c 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0dpd-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0dpd-1.c
@@ -12,6 +12,6 @@ void *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_prefetch_i32scatter_pd (base, idx, 8, 1);
-  _mm512_mask_prefetch_i32scatter_pd (base, m8, idx, 8, 5);
+  _mm512_prefetch_i32scatter_pd (base, idx, 8, _MM_HINT_T0);
+  _mm512_mask_prefetch_i32scatter_pd (base, m8, idx, 8, _MM_HINT_ET0);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0dps-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0dps-1.c
index 25448b4e2f4065822ba928488792126c6cd40dec..05f51f2bc805abfec7faea11e1bb18b0ee861dfc 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0dps-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0dps-1.c
@@ -12,6 +12,6 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_prefetch_i32scatter_ps (base, idx, 8, 1);
-  _mm512_mask_prefetch_i32scatter_ps (base, m16, idx, 8, 5);
+  _mm512_prefetch_i32scatter_ps (base, idx, 8, _MM_HINT_T0);
+  _mm512_mask_prefetch_i32scatter_ps (base, m16, idx, 8, _MM_HINT_ET0);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0qpd-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0qpd-1.c
index 84ddc6d9b9667bd516a1cf413972e467b759d8b6..93a65a8c17027e710b50c4d644f1ff3eee0d0d71 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0qpd-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0qpd-1.c
@@ -12,6 +12,6 @@ void *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_prefetch_i64scatter_pd (base, idx, 8, 1);
-  _mm512_mask_prefetch_i64scatter_pd (base, m8, idx, 8, 5);
+  _mm512_prefetch_i64scatter_pd (base, idx, 8, _MM_HINT_T0);
+  _mm512_mask_prefetch_i64scatter_pd (base, m8, idx, 8, _MM_HINT_ET0);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0qps-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0qps-1.c
index 847a719371f2a9ff095f0fdc9e2823e0dd95a197..1f9b97363a38d9efc2b7f99ef1d9975c9733ac71 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0qps-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf0qps-1.c
@@ -12,6 +12,6 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_prefetch_i64scatter_ps (base, idx, 8, 1);
-  _mm512_mask_prefetch_i64scatter_ps (base, m8, idx, 8, 5);
+  _mm512_prefetch_i64scatter_ps (base, idx, 8, _MM_HINT_T0);
+  _mm512_mask_prefetch_i64scatter_ps (base, m8, idx, 8, _MM_HINT_ET0);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1dpd-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1dpd-1.c
index 5633138825fab38c068c22184d0ee2cdd023e358..04c367ca3f0f84db740a717876a4f00955f5b4bb 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1dpd-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1dpd-1.c
@@ -12,6 +12,6 @@ void *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_prefetch_i32scatter_pd (base, idx, 8, 2);
-  _mm512_mask_prefetch_i32scatter_pd (base, m8, idx, 8, 6);
+  _mm512_prefetch_i32scatter_pd (base, idx, 8, _MM_HINT_T1);
+  _mm512_mask_prefetch_i32scatter_pd (base, m8, idx, 8, _MM_HINT_ET1);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1dps-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1dps-1.c
index fb70439859447c104c520887c40cc8c48e16c8ff..a76b77c635cfbf15eb3b9394bf5b3b1c65c02bef 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1dps-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1dps-1.c
@@ -12,6 +12,6 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_prefetch_i32scatter_ps (base, idx, 8, 2);
-  _mm512_mask_prefetch_i32scatter_ps (base, m16, idx, 8, 6);
+  _mm512_prefetch_i32scatter_ps (base, idx, 8, _MM_HINT_T1);
+  _mm512_mask_prefetch_i32scatter_ps (base, m16, idx, 8, _MM_HINT_ET1);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1qpd-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1qpd-1.c
index 7fbd1429cf7e0cfa4558b3203120ca77b039fd4a..7a5747cfe5991d129fbb4cb50265d56d3de01ab7 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1qpd-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1qpd-1.c
@@ -12,6 +12,6 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_prefetch_i64scatter_pd (base, idx, 8, 2);
-  _mm512_mask_prefetch_i64scatter_pd (base, m8, idx, 8, 6);
+  _mm512_prefetch_i64scatter_pd (base, idx, 8, _MM_HINT_T1);
+  _mm512_mask_prefetch_i64scatter_pd (base, m8, idx, 8, _MM_HINT_ET1);
 }

diff --git a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1qps-1.c b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1qps-1.c
index c0048341f045c99ecca390133b2bf80b43b1209a..d0372b7b3e7ab4a429be291a6880b8fb6459d983 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1qps-1.c
+++ b/gcc/testsuite/gcc.target/i386/avx512pf-vscatterpf1qps-1.c
@@ -12,6 +12,6 @@ int *base;
 void extern
 avx512pf_test (void)
 {
-  _mm512_prefetch_i64scatter_ps (base, idx, 8, 2);
-  _mm512_mask_prefetch_i64scatter_ps (base, m8, idx, 8, 6);
+  _mm512_prefetch_i64scatter_ps (base, idx, 8, _MM_HINT_T1);
+  _mm512_mask_prefetch_i64scatter_ps (base, m8, idx, 8, _MM_HINT_ET1);
 }

diff --git a/gcc/testsuite/gcc.target/i386/sse-14.c b/gcc/testsuite/gcc.target/i386/sse-14.c
index 10334a6bcac8ce535ab45fe2abfe33e0fd079dc9..d9a5feddaeab1c896561a599b37d0e874176dcab 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/sse-14.c
+++ b/gcc/testsuite/gcc.target/i386/sse-14.c
@@ -519,14 +519,14 @@ test_4x (_mm_maskz_fixupimm_round_sd, __m128d, __mmask8, __m128d, __m128d, __m12
 test_4x (_mm_maskz_fixupimm_round_ss, __m128, __mmask8, __m128, __m128, __m128i, 1, 8)
 
 /* avx512pfintrin.h */
-test_3vx (_mm512_mask_prefetch_i32gather_ps, __m512i, __mmask16, void const *, 1, 1)
-test_3vx (_mm512_mask_prefetch_i32scatter_ps, void const *, __mmask16, __m512i, 1, 1)
-test_3vx (_mm512_mask_prefetch_i64gather_ps, __m512i, __mmask8, void const *, 1, 1)
-test_3vx (_mm512_mask_prefetch_i64scatter_ps, void const *, __mmask8, __m512i, 1, 1)
-test_3vx (_mm512_mask_prefetch_i32gather_pd, __m256i, __mmask8, void const *, 1, 1)
-test_3vx (_mm512_mask_prefetch_i32scatter_pd, void const *, __mmask8, __m256i, 1, 1)
-test_3vx (_mm512_mask_prefetch_i64gather_pd, __m512i, __mmask8, void const *, 1, 1)
-test_3vx (_mm512_mask_prefetch_i64scatter_pd, void const *, __mmask8, __m512i, 1, 1)
+test_3vx (_mm512_mask_prefetch_i32gather_ps, __m512i, __mmask16, void const *, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i32scatter_ps, void const *, __mmask16, __m512i, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i64gather_ps, __m512i, __mmask8, void const *, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i64scatter_ps, void const *, __mmask8, __m512i, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i32gather_pd, __m256i, __mmask8, void const *, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i32scatter_pd, void const *, __mmask8, __m256i, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i64gather_pd, __m512i, __mmask8, void const *, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i64scatter_pd, void const *, __mmask8, __m512i, 1, _MM_HINT_T0)
 
 /* avx512erintrin.h */
 test_1 (_mm512_exp2a23_round_pd, __m512d, __m512d, 8)

diff --git a/gcc/testsuite/gcc.target/i386/sse-22.c b/gcc/testsuite/gcc.target/i386/sse-22.c
index 51f04c230de602cf3f039cc921ddbd84fd30a337..e9f227a2a81a21453299432a46828f429a5f0528 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/sse-22.c
+++ b/gcc/testsuite/gcc.target/i386/sse-22.c
@@ -641,15 +641,15 @@ test_4x (_mm_maskz_fixupimm_round_sd, __m128d, __mmask8, __m128d, __m128d, __m12
 test_4x (_mm_maskz_fixupimm_round_ss, __m128, __mmask8, __m128, __m128, __m128i, 1, 8)
 
 /* avx512pfintrin.h */
-test_3vx (_mm512_mask_prefetch_i32gather_ps, __m512i, __mmask16, void const *, 1, 1)
-test_3vx (_mm512_mask_prefetch_i32scatter_ps, void const *, __mmask16, __m512i, 1, 1)
-test_3vx (_mm512_mask_prefetch_i64gather_ps, __m512i, __mmask8, void const *, 1, 1)
-test_3vx (_mm512_mask_prefetch_i64scatter_ps, void const *, __mmask8, __m512i, 1, 1)
-
-test_3vx (_mm512_mask_prefetch_i32gather_pd, __m256i, __mmask8, void const *, 1, 1)
-test_3vx (_mm512_mask_prefetch_i32scatter_pd, void const *, __mmask8, __m256i, 1, 1)
-test_3vx (_mm512_mask_prefetch_i64gather_pd, __m512i, __mmask8, long long *, 1, 1)
-test_3vx (_mm512_mask_prefetch_i64scatter_pd, void const *, __mmask8, __m512i, 1, 1)
+test_3vx (_mm512_mask_prefetch_i32gather_ps, __m512i, __mmask16, void const *, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i32scatter_ps, void const *, __mmask16, __m512i, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i64gather_ps, __m512i, __mmask8, void const *, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i64scatter_ps, void const *, __mmask8, __m512i, 1, _MM_HINT_T0)
+
+test_3vx (_mm512_mask_prefetch_i32gather_pd, __m256i, __mmask8, void const *, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i32scatter_pd, void const *, __mmask8, __m256i, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i64gather_pd, __m512i, __mmask8, long long *, 1, _MM_HINT_T0)
+test_3vx (_mm512_mask_prefetch_i64scatter_pd, void const *, __mmask8, __m512i, 1, _MM_HINT_T0)
 
 /* avx512erintrin.h */
 test_1 (_mm512_exp2a23_round_pd, __m512d, __m512d, 8)

diff --git a/gcc/testsuite/gcc.target/i386/sse-23.c b/gcc/testsuite/gcc.target/i386/sse-23.c
index 5b24618ec74c0180169cb57c4265e40353579613..d227babb8cb5696e5efa06be63130b21829c337c 100644 (file)
--- a/gcc/testsuite/gcc.target/i386/sse-23.c
+++ b/gcc/testsuite/gcc.target/i386/sse-23.c
@@ -361,14 +361,14 @@
 #define __builtin_ia32_vpermilps512_mask(A, E, C, D) __builtin_ia32_vpermilps512_mask(A, 1, C, D)
 
 /* avx512pfintrin.h */
-#define __builtin_ia32_gatherpfdps(A, B, C, D, E) __builtin_ia32_gatherpfdps(A, B, C, 1, 1)
-#define __builtin_ia32_gatherpfqps(A, B, C, D, E) __builtin_ia32_gatherpfqps(A, B, C, 1, 1)
-#define __builtin_ia32_scatterpfdps(A, B, C, D, E) __builtin_ia32_scatterpfdps(A, B, C, 1, 1)
-#define __builtin_ia32_scatterpfqps(A, B, C, D, E) __builtin_ia32_scatterpfqps(A, B, C, 1, 1)
-#define __builtin_ia32_gatherpfdpd(A, B, C, D, E) __builtin_ia32_gatherpfdpd(A, B, C, 1, 1)
-#define __builtin_ia32_gatherpfqpd(A, B, C, D, E) __builtin_ia32_gatherpfqpd(A, B, C, 1, 1)
-#define __builtin_ia32_scatterpfdpd(A, B, C, D, E) __builtin_ia32_scatterpfdpd(A, B, C, 1, 1)
-#define __builtin_ia32_scatterpfqpd(A, B, C, D, E) __builtin_ia32_scatterpfqpd(A, B, C, 1, 1)
+#define __builtin_ia32_gatherpfdps(A, B, C, D, E) __builtin_ia32_gatherpfdps(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_gatherpfqps(A, B, C, D, E) __builtin_ia32_gatherpfqps(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_scatterpfdps(A, B, C, D, E) __builtin_ia32_scatterpfdps(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_scatterpfqps(A, B, C, D, E) __builtin_ia32_scatterpfqps(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_gatherpfdpd(A, B, C, D, E) __builtin_ia32_gatherpfdpd(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_gatherpfqpd(A, B, C, D, E) __builtin_ia32_gatherpfqpd(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_scatterpfdpd(A, B, C, D, E) __builtin_ia32_scatterpfdpd(A, B, C, 1, _MM_HINT_T0)
+#define __builtin_ia32_scatterpfqpd(A, B, C, D, E) __builtin_ia32_scatterpfqpd(A, B, C, 1, _MM_HINT_T0)
 
 /* avx512erintrin.h */
 #define __builtin_ia32_exp2pd_mask(A, B, C, D) __builtin_ia32_exp2pd_mask (A, B, C, 8)