[PATCH 2/3] Change internal intrin call for AVX512 intrins

gcc/ChangeLog:

	* config/i386/avx512bf16vlintrin.h: Change intrin call.
	* config/i386/avx512fintrin.h
	(_mm_avx512_undefined_ps): New.
	(_mm_avx512_undefined_pd): Ditto.
	(__attribute__): Change intrin call.
	* config/i386/avx512vbmivlintrin.h: Ditto.
	* config/i386/avx512vlbwintrin.h: Ditto.
	* config/i386/avx512vldqintrin.h: Ditto.
	* config/i386/avx512vlintrin.h
	(_mm_avx512_undefined_si128): New.
	(_mm256_avx512_undefined_ps): Ditto.
	(_mm256_avx512_undefined_pd): Ditto.
	(_mm256_avx512_undefined_si256): Ditto.
	(__attribute__): Change intrin call.

diff --git a/gcc/config/i386/avx512bf16vlintrin.h b/gcc/config/i386/avx512bf16vlintrin.h
index 6e8a6a095110ad0981ac01ad04720b605c1973b0..517544c5b89a704966cf7f195c94ac40dc61eb83 100644 (file)
--- a/gcc/config/i386/avx512bf16vlintrin.h
+++ b/gcc/config/i386/avx512bf16vlintrin.h
@@ -174,7 +174,7 @@ _mm_cvtness_sbh (float __A)
 {
   __v4sf __V = {__A, 0, 0, 0};
   __v8bf __R = __builtin_ia32_cvtneps2bf16_v4sf_mask ((__v4sf)__V,
-              (__v8bf)_mm_undefined_si128 (), (__mmask8)-1);
+              (__v8bf)_mm_avx512_undefined_si128 (), (__mmask8)-1);
   return __R[0];
 }
 

diff --git a/gcc/config/i386/avx512fintrin.h b/gcc/config/i386/avx512fintrin.h
index 530be29eefa32fc932ccfebd75f037405a41defb..90a00bec09a896183948fae31d63691910c55bc4 100644 (file)
--- a/gcc/config/i386/avx512fintrin.h
+++ b/gcc/config/i386/avx512fintrin.h
@@ -59,6 +59,26 @@ typedef enum
    when calling AVX512 intrins implemented with these intrins under no-evex512
    function attribute.  All AVX512 intrins calling those AVX2 intrins or
    before will change their calls to these AVX512 version.  */
+extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm_avx512_undefined_ps (void)
+{
+#pragma GCC diagnostic push
+#pragma GCC diagnostic ignored "-Winit-self"
+  __m128 __Y = __Y;
+#pragma GCC diagnostic pop
+  return __Y;
+}
+
+extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm_avx512_undefined_pd (void)
+{
+#pragma GCC diagnostic push
+#pragma GCC diagnostic ignored "-Winit-self"
+  __m128d __Y = __Y;
+#pragma GCC diagnostic pop
+  return __Y;
+}
+
 extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 _mm_avx512_setzero_ps (void)
 {
@@ -674,13 +694,13 @@ _mm_maskz_scalef_round_ss (__mmask8 __U, __m128 __A, __m128 __B, const int __R)
 #define _mm_scalef_round_sd(A, B, C)                                   \
   ((__m128d)                                                           \
    __builtin_ia32_scalefsd_mask_round ((A), (B),                       \
-                                      (__v2df) _mm_undefined_pd (),    \
+                                      (__v2df) _mm_avx512_undefined_pd (),     \
                                       -1, (C)))
 
 #define _mm_scalef_round_ss(A, B, C)                                   \
   ((__m128)                                                            \
    __builtin_ia32_scalefss_mask_round ((A), (B),                       \
-                                      (__v4sf) _mm_undefined_ps (),    \
+                                      (__v4sf) _mm_avx512_undefined_ps (),     \
                                       -1, (C)))
 
 #define _mm_mask_scalef_round_sd(W, U, A, B, C)                                \

diff --git a/gcc/config/i386/avx512vbmivlintrin.h b/gcc/config/i386/avx512vbmivlintrin.h
index 270e9406db5eab2f4395f1b4c27a0078b3cb5bc5..acec23b742f848c4214968e10892a8d25944d51d 100644 (file)
--- a/gcc/config/i386/avx512vbmivlintrin.h
+++ b/gcc/config/i386/avx512vbmivlintrin.h
@@ -62,7 +62,7 @@ _mm256_multishift_epi64_epi8 (__m256i __X, __m256i __Y)
   return (__m256i) __builtin_ia32_vpmultishiftqb256_mask ((__v32qi) __X,
                                                          (__v32qi) __Y,
                                                          (__v32qi)
-                                                         _mm256_undefined_si256 (),
+                                                         _mm256_avx512_undefined_si256 (),
                                                          (__mmask32) -1);
 }
 
@@ -94,7 +94,7 @@ _mm_multishift_epi64_epi8 (__m128i __X, __m128i __Y)
   return (__m128i) __builtin_ia32_vpmultishiftqb128_mask ((__v16qi) __X,
                                                          (__v16qi) __Y,
                                                          (__v16qi)
-                                                         _mm_undefined_si128 (),
+                                                         _mm_avx512_undefined_si128 (),
                                                          (__mmask16) -1);
 }
 
@@ -105,7 +105,7 @@ _mm256_permutexvar_epi8 (__m256i __A, __m256i __B)
   return (__m256i) __builtin_ia32_permvarqi256_mask ((__v32qi) __B,
                                                     (__v32qi) __A,
                                                     (__v32qi)
-                                                    _mm256_undefined_si256 (),
+                                                    _mm256_avx512_undefined_si256 (),
                                                     (__mmask32) -1);
 }
 
@@ -139,7 +139,7 @@ _mm_permutexvar_epi8 (__m128i __A, __m128i __B)
   return (__m128i) __builtin_ia32_permvarqi128_mask ((__v16qi) __B,
                                                     (__v16qi) __A,
                                                     (__v16qi)
-                                                    _mm_undefined_si128 (),
+                                                    _mm_avx512_undefined_si128 (),
                                                     (__mmask16) -1);
 }
 

diff --git a/gcc/config/i386/avx512vlbwintrin.h b/gcc/config/i386/avx512vlbwintrin.h
index 7654bfaa87eef5704d2324f4bf9895359c1e8b59..d7c8ea46df8112667fb3d24ca3fe2453c104c36f 100644 (file)
--- a/gcc/config/i386/avx512vlbwintrin.h
+++ b/gcc/config/i386/avx512vlbwintrin.h
@@ -299,7 +299,7 @@ _mm256_cvtepi16_epi8 (__m256i __A)
 {
 
   return (__m128i) __builtin_ia32_pmovwb256_mask ((__v16hi) __A,
-                                                 (__v16qi)_mm_undefined_si128(),
+                                                 (__v16qi)_mm_avx512_undefined_si128(),
                                                  (__mmask16) -1);
 }
 
@@ -334,7 +334,7 @@ _mm_cvtsepi16_epi8 (__m128i __A)
 {
 
   return (__m128i) __builtin_ia32_pmovswb128_mask ((__v8hi) __A,
-                                                  (__v16qi)_mm_undefined_si128(),
+                                                  (__v16qi)_mm_avx512_undefined_si128(),
                                                   (__mmask8) -1);
 }
 
@@ -369,7 +369,7 @@ _mm256_cvtsepi16_epi8 (__m256i __A)
 {
 
   return (__m128i) __builtin_ia32_pmovswb256_mask ((__v16hi) __A,
-                                                  (__v16qi)_mm_undefined_si128(),
+                                                  (__v16qi)_mm_avx512_undefined_si128(),
                                                   (__mmask16) -1);
 }
 
@@ -404,7 +404,7 @@ _mm_cvtusepi16_epi8 (__m128i __A)
 {
 
   return (__m128i) __builtin_ia32_pmovuswb128_mask ((__v8hi) __A,
-                                                   (__v16qi)_mm_undefined_si128(),
+                                                   (__v16qi)_mm_avx512_undefined_si128(),
                                                    (__mmask8) -1);
 }
 
@@ -440,7 +440,7 @@ _mm256_cvtusepi16_epi8 (__m256i __A)
 {
 
   return (__m128i) __builtin_ia32_pmovuswb256_mask ((__v16hi) __A,
-                                                   (__v16qi)_mm_undefined_si128(),
+                                                   (__v16qi)_mm_avx512_undefined_si128(),
                                                    (__mmask16) -1);
 }
 
@@ -4089,7 +4089,7 @@ _mm_cvtepi16_epi8 (__m128i __A)
 {
 
   return (__m128i) __builtin_ia32_pmovwb128_mask ((__v8hi) __A,
-                                                 (__v16qi)_mm_undefined_si128(),
+                                                 (__v16qi)_mm_avx512_undefined_si128(),
                                                  (__mmask8) -1);
 }
 

diff --git a/gcc/config/i386/avx512vldqintrin.h b/gcc/config/i386/avx512vldqintrin.h
index 7bb87bbd9be93717a62ac871b5e5d89b1e778518..1949737fe9cb0ae76b7250403c6ae89b195b4b01 100644 (file)
--- a/gcc/config/i386/avx512vldqintrin.h
+++ b/gcc/config/i386/avx512vldqintrin.h
@@ -388,7 +388,7 @@ _mm256_broadcast_f64x2 (__m128d __A)
 {
   return (__m256d) __builtin_ia32_broadcastf64x2_256_mask ((__v2df)
                                                           __A,
-                                                          (__v4df)_mm256_undefined_pd(),
+                                                          (__v4df)_mm256_avx512_undefined_pd(),
                                                           (__mmask8) -1);
 }
 
@@ -419,7 +419,7 @@ _mm256_broadcast_i64x2 (__m128i __A)
 {
   return (__m256i) __builtin_ia32_broadcasti64x2_256_mask ((__v2di)
                                                           __A,
-                                                          (__v4di)_mm256_undefined_si256(),
+                                                          (__v4di)_mm256_avx512_undefined_si256(),
                                                           (__mmask8) -1);
 }
 
@@ -449,7 +449,7 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
 _mm256_broadcast_f32x2 (__m128 __A)
 {
   return (__m256) __builtin_ia32_broadcastf32x2_256_mask ((__v4sf) __A,
-                                                         (__v8sf)_mm256_undefined_ps(),
+                                                         (__v8sf)_mm256_avx512_undefined_ps(),
                                                          (__mmask8) -1);
 }
 
@@ -478,7 +478,7 @@ _mm256_broadcast_i32x2 (__m128i __A)
 {
   return (__m256i) __builtin_ia32_broadcasti32x2_256_mask ((__v4si)
                                                           __A,
-                                                         (__v8si)_mm256_undefined_si256(),
+                                                         (__v8si)_mm256_avx512_undefined_si256(),
                                                           (__mmask8) -1);
 }
 
@@ -509,7 +509,7 @@ _mm_broadcast_i32x2 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_broadcasti32x2_128_mask ((__v4si)
                                                           __A,
-                                                         (__v4si)_mm_undefined_si128(),
+                                                         (__v4si)_mm_avx512_undefined_si128(),
                                                           (__mmask8) -1);
 }
 

diff --git a/gcc/config/i386/avx512vlintrin.h b/gcc/config/i386/avx512vlintrin.h
index 2b33b82b7ef6acb75a9945f9faa89504d07851dc..d4932f29b56d0828515d49419311aca6d85c6329 100644 (file)
--- a/gcc/config/i386/avx512vlintrin.h
+++ b/gcc/config/i386/avx512vlintrin.h
@@ -46,15 +46,49 @@ typedef long long __v4di_u __attribute__ ((__vector_size__ (32),    \
                                           __may_alias__, __aligned__ (1)));
 
 extern __inline __m128i __attribute__((__gnu_inline__, __always_inline__, __artificial__))
-_mm_avx512_setzero_si128 (void)
+_mm_avx512_undefined_si128 (void)
 {
-  return __extension__ (__m128i)(__v4si){ 0, 0, 0, 0 };
+#pragma GCC diagnostic push
+#pragma GCC diagnostic ignored "-Winit-self"
+  __m128i __Y = __Y;
+#pragma GCC diagnostic pop
+  return __Y;
+}
+
+extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm256_avx512_undefined_ps (void)
+{
+#pragma GCC diagnostic push
+#pragma GCC diagnostic ignored "-Winit-self"
+  __m256 __Y = __Y;
+#pragma GCC diagnostic pop
+  return __Y;
 }
 
 extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
-_mm256_avx512_setzero_pd (void)
+_mm256_avx512_undefined_pd (void)
 {
-  return __extension__ (__m256d){ 0.0, 0.0, 0.0, 0.0 };
+#pragma GCC diagnostic push
+#pragma GCC diagnostic ignored "-Winit-self"
+  __m256d __Y = __Y;
+#pragma GCC diagnostic pop
+  return __Y;
+}
+
+extern __inline __m256i __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm256_avx512_undefined_si256 (void)
+{
+#pragma GCC diagnostic push
+#pragma GCC diagnostic ignored "-Winit-self"
+  __m256i __Y = __Y;
+#pragma GCC diagnostic pop
+  return __Y;
+}
+
+extern __inline __m128i __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm_avx512_setzero_si128 (void)
+{
+  return __extension__ (__m128i)(__v4si){ 0, 0, 0, 0 };
 }
 
 extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
@@ -64,6 +98,12 @@ _mm256_avx512_setzero_ps (void)
                                 0.0, 0.0, 0.0, 0.0 };
 }
 
+extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm256_avx512_setzero_pd (void)
+{
+  return __extension__ (__m256d){ 0.0, 0.0, 0.0, 0.0 };
+}
+
 extern __inline __m256i __attribute__((__gnu_inline__, __always_inline__, __artificial__))
 _mm256_avx512_setzero_si256 (void)
 {
@@ -1652,7 +1692,7 @@ _mm_cvtepi32_epi8 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovdb128_mask ((__v4si) __A,
                                                  (__v16qi)
-                                                 _mm_undefined_si128 (),
+                                                 _mm_avx512_undefined_si128 (),
                                                  (__mmask8) -1);
 }
 
@@ -1687,7 +1727,7 @@ _mm256_cvtepi32_epi8 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovdb256_mask ((__v8si) __A,
                                                  (__v16qi)
-                                                 _mm_undefined_si128 (),
+                                                 _mm_avx512_undefined_si128 (),
                                                  (__mmask8) -1);
 }
 
@@ -1722,7 +1762,7 @@ _mm_cvtsepi32_epi8 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovsdb128_mask ((__v4si) __A,
                                                   (__v16qi)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -1757,7 +1797,7 @@ _mm256_cvtsepi32_epi8 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovsdb256_mask ((__v8si) __A,
                                                   (__v16qi)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -1792,7 +1832,7 @@ _mm_cvtusepi32_epi8 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovusdb128_mask ((__v4si) __A,
                                                    (__v16qi)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -1828,7 +1868,7 @@ _mm256_cvtusepi32_epi8 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovusdb256_mask ((__v8si) __A,
                                                    (__v16qi)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -1970,7 +2010,7 @@ _mm256_cvtsepi32_epi16 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovsdw256_mask ((__v8si) __A,
                                                   (__v8hi)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -2005,7 +2045,7 @@ _mm_cvtusepi32_epi16 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovusdw128_mask ((__v4si) __A,
                                                    (__v8hi)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -2040,7 +2080,7 @@ _mm256_cvtusepi32_epi16 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovusdw256_mask ((__v8si) __A,
                                                    (__v8hi)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -2075,7 +2115,7 @@ _mm_cvtepi64_epi8 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovqb128_mask ((__v2di) __A,
                                                  (__v16qi)
-                                                 _mm_undefined_si128 (),
+                                                 _mm_avx512_undefined_si128 (),
                                                  (__mmask8) -1);
 }
 
@@ -2110,7 +2150,7 @@ _mm256_cvtepi64_epi8 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovqb256_mask ((__v4di) __A,
                                                  (__v16qi)
-                                                 _mm_undefined_si128 (),
+                                                 _mm_avx512_undefined_si128 (),
                                                  (__mmask8) -1);
 }
 
@@ -2145,7 +2185,7 @@ _mm_cvtsepi64_epi8 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovsqb128_mask ((__v2di) __A,
                                                   (__v16qi)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -2180,7 +2220,7 @@ _mm256_cvtsepi64_epi8 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovsqb256_mask ((__v4di) __A,
                                                   (__v16qi)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -2215,7 +2255,7 @@ _mm_cvtusepi64_epi8 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovusqb128_mask ((__v2di) __A,
                                                    (__v16qi)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -2251,7 +2291,7 @@ _mm256_cvtusepi64_epi8 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovusqb256_mask ((__v4di) __A,
                                                    (__v16qi)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -2287,7 +2327,7 @@ _mm_cvtepi64_epi16 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovqw128_mask ((__v2di) __A,
                                                  (__v8hi)
-                                                 _mm_undefined_si128 (),
+                                                 _mm_avx512_undefined_si128 (),
                                                  (__mmask8) -1);
 }
 
@@ -2323,7 +2363,7 @@ _mm256_cvtepi64_epi16 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovqw256_mask ((__v4di) __A,
                                                  (__v8hi)
-                                                 _mm_undefined_si128 (),
+                                                 _mm_avx512_undefined_si128 (),
                                                  (__mmask8) -1);
 }
 
@@ -2358,7 +2398,7 @@ _mm_cvtsepi64_epi16 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovsqw128_mask ((__v2di) __A,
                                                   (__v8hi)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -2393,7 +2433,7 @@ _mm256_cvtsepi64_epi16 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovsqw256_mask ((__v4di) __A,
                                                   (__v8hi)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -2428,7 +2468,7 @@ _mm_cvtusepi64_epi16 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovusqw128_mask ((__v2di) __A,
                                                    (__v8hi)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -2463,7 +2503,7 @@ _mm256_cvtusepi64_epi16 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovusqw256_mask ((__v4di) __A,
                                                    (__v8hi)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -2498,7 +2538,7 @@ _mm_cvtepi64_epi32 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovqd128_mask ((__v2di) __A,
                                                  (__v4si)
-                                                 _mm_undefined_si128 (),
+                                                 _mm_avx512_undefined_si128 (),
                                                  (__mmask8) -1);
 }
 
@@ -2534,7 +2574,7 @@ _mm256_cvtepi64_epi32 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovqd256_mask ((__v4di) __A,
                                                  (__v4si)
-                                                 _mm_undefined_si128 (),
+                                                 _mm_avx512_undefined_si128 (),
                                                  (__mmask8) -1);
 }
 
@@ -2569,7 +2609,7 @@ _mm_cvtsepi64_epi32 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovsqd128_mask ((__v2di) __A,
                                                   (__v4si)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -2604,7 +2644,7 @@ _mm256_cvtsepi64_epi32 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovsqd256_mask ((__v4di) __A,
                                                   (__v4si)
-                                                  _mm_undefined_si128 (),
+                                                  _mm_avx512_undefined_si128 (),
                                                   (__mmask8) -1);
 }
 
@@ -2640,7 +2680,7 @@ _mm_cvtusepi64_epi32 (__m128i __A)
 {
   return (__m128i) __builtin_ia32_pmovusqd128_mask ((__v2di) __A,
                                                    (__v4si)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -2675,7 +2715,7 @@ _mm256_cvtusepi64_epi32 (__m256i __A)
 {
   return (__m128i) __builtin_ia32_pmovusqd256_mask ((__v4di) __A,
                                                    (__v4si)
-                                                   _mm_undefined_si128 (),
+                                                   _mm_avx512_undefined_si128 (),
                                                    (__mmask8) -1);
 }
 
@@ -2914,7 +2954,7 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
 _mm256_broadcast_f32x4 (__m128 __A)
 {
   return (__m256) __builtin_ia32_broadcastf32x4_256_mask ((__v4sf) __A,
-                                                         (__v8sf)_mm256_undefined_pd (),
+                                                         (__v8sf)_mm256_avx512_undefined_pd (),
                                                          (__mmask8) -1);
 }
 
@@ -2943,7 +2983,7 @@ _mm256_broadcast_i32x4 (__m128i __A)
 {
   return (__m256i) __builtin_ia32_broadcasti32x4_256_mask ((__v4si)
                                                           __A,
-                                                          (__v8si)_mm256_undefined_si256 (),
+                                                          (__v8si)_mm256_avx512_undefined_si256 (),
                                                           (__mmask8) -1);
 }
 
@@ -12315,7 +12355,7 @@ _mm256_permutex_pd (__m256d __X, const int __M)
 {
   return (__m256d) __builtin_ia32_permdf256_mask ((__v4df) __X, __M,
                                                  (__v4df)
-                                                 _mm256_undefined_pd (),
+                                                 _mm256_avx512_undefined_pd (),
                                                  (__mmask8) -1);
 }
 
@@ -12323,7 +12363,7 @@ _mm256_permutex_pd (__m256d __X, const int __M)
 #define _mm256_permutex_pd(X, M)                                               \
   ((__m256d) __builtin_ia32_permdf256_mask ((__v4df)(__m256d)(X), (int)(M),    \
                                            (__v4df)(__m256d)                   \
-                                           _mm256_undefined_pd (),             \
+                                           _mm256_avx512_undefined_pd (),              \
                                            (__mmask8)-1))
 
 #define _mm256_permutex_epi64(X, I)               \