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.
---
gcc/config/i386/avx512bf16vlintrin.h | 2 +-
gcc/config/i386/avx512fintrin.h | 24 +++++-
gcc/config/i386/avx512vbmivlintrin.h | 8 +-
gcc/config/i386/avx512vlbwintrin.h | 12 +--
gcc/config/i386/avx512vldqintrin.h | 10 +--
gcc/config/i386/avx512vlintrin.h | 110 ++++++++++++++++++---------
6 files changed, 113 insertions(+), 53 deletions(-)
diff --git a/gcc/config/i386/avx512bf16vlintrin.h
b/gcc/config/i386/avx512bf16vlintrin.h
index 6e8a6a09511..517544c5b89 100644
--- 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 530be29eefa..90a00bec09a 100644
--- 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 270e9406db5..acec23b742f 100644
--- 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 7654bfaa87e..d7c8ea46df8 100644
--- 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 7bb87bbd9be..1949737fe9c 100644
--- 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 2b33b82b7ef..d4932f29b56 100644
--- 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) \
--
2.31.1
