[PATCH] x86: _mm*_undefined_* (for real)
Ulrich Drepper
drepper@gmail.com
Fri Mar 21 11:39:00 GMT 2014
This is a tested version of the patch I sent before. I'm using the
type var = var
trick for the initialization so far even those this is not ideal as I
have shown in one of the emails before. If anyone could work on a real
solution we could get even better code generation.
In the meantime, the patch should be fine. I've bootstrapped the
compiler on x86-64. The patch adds the _mm*_undefined_* definitions and
uses them where appropriate. Most of the related changes are cleanups.
In some cases completely uninitialized variables are used and I consider
that code buggy. So the patch is actually also a bug fix.
2014-03-19 Ulrich Drepper <drepper@gmail.com>
* config/i386/avxintrin.h (_mm256_undefined_si256): Define.
(_mm256_undefined_ps): Define.
(_mm256_undefined_pd): Define.
* config/i386/emmintrin.h (_mm_undefined_si128): Define.
(_mm_undefined_pd): Define.
* config/i386/xmmintrin.h (_mm_undefined_ps): Define.
* config/i386/avx512fintrin.h (_mm512_undefined_si512): Define.
(_mm512_undefined_ps): Define.
(_mm512_undefined_pd): Define.
Use _mm*_undefined_*.
* config/i386/avx2intrin.h: Use _mm*_undefined_*.
Anyone having a problem with the patch? If not, should this patch wait
until after the release? I found a few more intrinsics which are
missing and I'll have more patches. From personal experience I find it
very frustrating if a gcc release doesn't have the complete set of
intrinsics since then you have to provide your own implementations in
code which doesn't assume the latest compiler.
diff --git a/gcc/config/i386/avx2intrin.h b/gcc/config/i386/avx2intrin.h
index 33b12e1..d04c972 100644
--- a/gcc/config/i386/avx2intrin.h
+++ b/gcc/config/i386/avx2intrin.h
@@ -1233,10 +1233,10 @@ extern __inline __m128d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm_i32gather_pd (double const *base, __m128i index, const int scale)
{
- __v2df src = _mm_setzero_pd ();
- __v2df mask = _mm_cmpeq_pd (src, src);
+ __v2df zero = _mm_setzero_pd ();
+ __v2df mask = _mm_cmpeq_pd (zero, zero);
- return (__m128d) __builtin_ia32_gathersiv2df (src,
+ return (__m128d) __builtin_ia32_gathersiv2df (_mm_undefined_pd (),
base,
(__v4si)index,
mask,
@@ -1259,10 +1259,10 @@ extern __inline __m256d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm256_i32gather_pd (double const *base, __m128i index, const int scale)
{
- __v4df src = _mm256_setzero_pd ();
- __v4df mask = _mm256_cmp_pd (src, src, _CMP_EQ_OQ);
+ __v4df zero = _mm256_setzero_pd ();
+ __v4df mask = _mm256_cmp_pd (zero, zero, _CMP_EQ_OQ);
- return (__m256d) __builtin_ia32_gathersiv4df (src,
+ return (__m256d) __builtin_ia32_gathersiv4df (_mm256_undefined_pd (),
base,
(__v4si)index,
mask,
diff --git a/gcc/config/i386/avx512fintrin.h b/gcc/config/i386/avx512fintrin.h
index 422e83b..20b3baf 100644
--- a/gcc/config/i386/avx512fintrin.h
+++ b/gcc/config/i386/avx512fintrin.h
@@ -108,6 +108,30 @@ _mm512_set_ps (float __A, float __B, float __C, float __D,
extern __inline __m512
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
+_mm512_undefined_ps (void)
+{
+ __m512 __Y = __Y;
+ return __Y;
+}
+
+extern __inline __m512d
+__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
+_mm512_undefined_pd (void)
+{
+ __m512d __Y = __Y;
+ return __Y;
+}
+
+extern __inline __m512i
+__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
+_mm512_undefined_si512 (void)
+{
+ __m512i __Y = __Y;
+ return __Y;
+}
+
+extern __inline __m512
+__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_setzero_ps (void)
{
return __extension__ (__m512){ 0.0, 0.0, 0.0, 0.0, 0.0, 0.0, 0.0, 0.0,
@@ -389,7 +413,7 @@ _mm512_mullo_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pmulld512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -420,7 +444,7 @@ _mm512_sllv_epi32 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_psllv16si_mask ((__v16si) __X,
(__v16si) __Y,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -452,7 +476,7 @@ _mm512_srav_epi32 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_psrav16si_mask ((__v16si) __X,
(__v16si) __Y,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -484,7 +508,7 @@ _mm512_srlv_epi32 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_psrlv16si_mask ((__v16si) __X,
(__v16si) __Y,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -516,7 +540,7 @@ _mm512_add_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_paddq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -548,7 +572,7 @@ _mm512_sub_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_psubq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -580,7 +604,7 @@ _mm512_sllv_epi64 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_psllv8di_mask ((__v8di) __X,
(__v8di) __Y,
(__v8di)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -612,7 +636,7 @@ _mm512_srav_epi64 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_psrav8di_mask ((__v8di) __X,
(__v8di) __Y,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -644,7 +668,7 @@ _mm512_srlv_epi64 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_psrlv8di_mask ((__v8di) __X,
(__v8di) __Y,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -676,7 +700,7 @@ _mm512_add_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_paddd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -708,7 +732,7 @@ _mm512_mul_epi32 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_pmuldq512_mask ((__v16si) __X,
(__v16si) __Y,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -739,7 +763,7 @@ _mm512_sub_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_psubd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -771,7 +795,7 @@ _mm512_mul_epu32 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_pmuludq512_mask ((__v16si) __X,
(__v16si) __Y,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -802,7 +826,7 @@ _mm512_slli_epi64 (__m512i __A, unsigned int __B)
{
return (__m512i) __builtin_ia32_psllqi512_mask ((__v8di) __A, __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -828,7 +852,7 @@ _mm512_maskz_slli_epi64 (__mmask8 __U, __m512i __A, unsigned int __B)
#else
#define _mm512_slli_epi64(X, C) \
((__m512i) __builtin_ia32_psllqi512_mask ((__v8di)(__m512i)(X), (int)(C),\
- (__v8di)(__m512i)_mm512_setzero_si512 (),\
+ (__v8di)(__m512i)_mm512_undefined_si512 (),\
(__mmask8)-1))
#define _mm512_mask_slli_epi64(W, U, X, C) \
@@ -849,7 +873,7 @@ _mm512_sll_epi64 (__m512i __A, __m128i __B)
return (__m512i) __builtin_ia32_psllq512_mask ((__v8di) __A,
(__v2di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -881,7 +905,7 @@ _mm512_srli_epi64 (__m512i __A, unsigned int __B)
{
return (__m512i) __builtin_ia32_psrlqi512_mask ((__v8di) __A, __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -907,7 +931,7 @@ _mm512_maskz_srli_epi64 (__mmask8 __U, __m512i __A, unsigned int __B)
#else
#define _mm512_srli_epi64(X, C) \
((__m512i) __builtin_ia32_psrlqi512_mask ((__v8di)(__m512i)(X), (int)(C),\
- (__v8di)(__m512i)_mm512_setzero_si512 (),\
+ (__v8di)(__m512i)_mm512_undefined_si512 (),\
(__mmask8)-1))
#define _mm512_mask_srli_epi64(W, U, X, C) \
@@ -928,7 +952,7 @@ _mm512_srl_epi64 (__m512i __A, __m128i __B)
return (__m512i) __builtin_ia32_psrlq512_mask ((__v8di) __A,
(__v2di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -960,7 +984,7 @@ _mm512_srai_epi64 (__m512i __A, unsigned int __B)
{
return (__m512i) __builtin_ia32_psraqi512_mask ((__v8di) __A, __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -986,7 +1010,7 @@ _mm512_maskz_srai_epi64 (__mmask8 __U, __m512i __A, unsigned int __B)
#else
#define _mm512_srai_epi64(X, C) \
((__m512i) __builtin_ia32_psraqi512_mask ((__v8di)(__m512i)(X), (int)(C),\
- (__v8di)(__m512i)_mm512_setzero_si512 (),\
+ (__v8di)(__m512i)_mm512_undefined_si512 (),\
(__mmask8)-1))
#define _mm512_mask_srai_epi64(W, U, X, C) \
@@ -1007,7 +1031,7 @@ _mm512_sra_epi64 (__m512i __A, __m128i __B)
return (__m512i) __builtin_ia32_psraq512_mask ((__v8di) __A,
(__v2di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -1039,7 +1063,7 @@ _mm512_slli_epi32 (__m512i __A, unsigned int __B)
{
return (__m512i) __builtin_ia32_pslldi512_mask ((__v16si) __A, __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1065,7 +1089,7 @@ _mm512_maskz_slli_epi32 (__mmask16 __U, __m512i __A, unsigned int __B)
#else
#define _mm512_slli_epi32(X, C) \
((__m512i) __builtin_ia32_pslldi512_mask ((__v16si)(__m512i)(X), (int)(C),\
- (__v16si)(__m512i)_mm512_setzero_si512 (),\
+ (__v16si)(__m512i)_mm512_undefined_si512 (),\
(__mmask16)-1))
#define _mm512_mask_slli_epi32(W, U, X, C) \
@@ -1086,7 +1110,7 @@ _mm512_sll_epi32 (__m512i __A, __m128i __B)
return (__m512i) __builtin_ia32_pslld512_mask ((__v16si) __A,
(__v4si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1118,7 +1142,7 @@ _mm512_srli_epi32 (__m512i __A, unsigned int __B)
{
return (__m512i) __builtin_ia32_psrldi512_mask ((__v16si) __A, __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1144,7 +1168,7 @@ _mm512_maskz_srli_epi32 (__mmask16 __U, __m512i __A, unsigned int __B)
#else
#define _mm512_srli_epi32(X, C) \
((__m512i) __builtin_ia32_psrldi512_mask ((__v16si)(__m512i)(X), (int)(C),\
- (__v16si)(__m512i)_mm512_setzero_si512 (),\
+ (__v16si)(__m512i)_mm512_undefined_si512 (),\
(__mmask16)-1))
#define _mm512_mask_srli_epi32(W, U, X, C) \
@@ -1165,7 +1189,7 @@ _mm512_srl_epi32 (__m512i __A, __m128i __B)
return (__m512i) __builtin_ia32_psrld512_mask ((__v16si) __A,
(__v4si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1197,7 +1221,7 @@ _mm512_srai_epi32 (__m512i __A, unsigned int __B)
{
return (__m512i) __builtin_ia32_psradi512_mask ((__v16si) __A, __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1223,7 +1247,7 @@ _mm512_maskz_srai_epi32 (__mmask16 __U, __m512i __A, unsigned int __B)
#else
#define _mm512_srai_epi32(X, C) \
((__m512i) __builtin_ia32_psradi512_mask ((__v16si)(__m512i)(X), (int)(C),\
- (__v16si)(__m512i)_mm512_setzero_si512 (),\
+ (__v16si)(__m512i)_mm512_undefined_si512 (),\
(__mmask16)-1))
#define _mm512_mask_srai_epi32(W, U, X, C) \
@@ -1244,7 +1268,7 @@ _mm512_sra_epi32 (__m512i __A, __m128i __B)
return (__m512i) __builtin_ia32_psrad512_mask ((__v16si) __A,
(__v4si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1414,7 +1438,7 @@ _mm512_rcp14_pd (__m512d __A)
{
return (__m512d) __builtin_ia32_rcp14pd512_mask ((__v8df) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -1443,7 +1467,7 @@ _mm512_rcp14_ps (__m512 __A)
{
return (__m512) __builtin_ia32_rcp14ps512_mask ((__v16sf) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -1488,7 +1512,7 @@ _mm512_rsqrt14_pd (__m512d __A)
{
return (__m512d) __builtin_ia32_rsqrt14pd512_mask ((__v8df) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -1517,7 +1541,7 @@ _mm512_rsqrt14_ps (__m512 __A)
{
return (__m512) __builtin_ia32_rsqrt14ps512_mask ((__v16sf) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -1563,7 +1587,7 @@ _mm512_sqrt_round_pd (__m512d __A, const int __R)
{
return (__m512d) __builtin_ia32_sqrtpd512_mask ((__v8df) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -1593,7 +1617,7 @@ _mm512_sqrt_round_ps (__m512 __A, const int __R)
{
return (__m512) __builtin_ia32_sqrtps512_mask ((__v16sf) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -1635,7 +1659,7 @@ _mm_sqrt_round_ss (__m128 __A, __m128 __B, const int __R)
}
#else
#define _mm512_sqrt_round_pd(A, C) \
- (__m512d)__builtin_ia32_sqrtpd512_mask(A, (__v8df)_mm512_setzero_pd(), -1, C)
+ (__m512d)__builtin_ia32_sqrtpd512_mask(A, (__v8df)_mm512_undefined_pd(), -1, C)
#define _mm512_mask_sqrt_round_pd(W, U, A, C) \
(__m512d)__builtin_ia32_sqrtpd512_mask(A, W, U, C)
@@ -1644,7 +1668,7 @@ _mm_sqrt_round_ss (__m128 __A, __m128 __B, const int __R)
(__m512d)__builtin_ia32_sqrtpd512_mask(A, (__v8df)_mm512_setzero_pd(), U, C)
#define _mm512_sqrt_round_ps(A, C) \
- (__m512)__builtin_ia32_sqrtps512_mask(A, (__v16sf)_mm512_setzero_ps(), -1, C)
+ (__m512)__builtin_ia32_sqrtps512_mask(A, (__v16sf)_mm512_undefined_ps(), -1, C)
#define _mm512_mask_sqrt_round_ps(W, U, A, C) \
(__m512)__builtin_ia32_sqrtps512_mask(A, W, U, C)
@@ -1665,7 +1689,7 @@ _mm512_cvtepi8_epi32 (__m128i __A)
{
return (__m512i) __builtin_ia32_pmovsxbd512_mask ((__v16qi) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1694,7 +1718,7 @@ _mm512_cvtepi8_epi64 (__m128i __A)
{
return (__m512i) __builtin_ia32_pmovsxbq512_mask ((__v16qi) __A,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -1723,7 +1747,7 @@ _mm512_cvtepi16_epi32 (__m256i __A)
{
return (__m512i) __builtin_ia32_pmovsxwd512_mask ((__v16hi) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1752,7 +1776,7 @@ _mm512_cvtepi16_epi64 (__m128i __A)
{
return (__m512i) __builtin_ia32_pmovsxwq512_mask ((__v8hi) __A,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -1781,7 +1805,7 @@ _mm512_cvtepi32_epi64 (__m256i __X)
{
return (__m512i) __builtin_ia32_pmovsxdq512_mask ((__v8si) __X,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -1810,7 +1834,7 @@ _mm512_cvtepu8_epi32 (__m128i __A)
{
return (__m512i) __builtin_ia32_pmovzxbd512_mask ((__v16qi) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1839,7 +1863,7 @@ _mm512_cvtepu8_epi64 (__m128i __A)
{
return (__m512i) __builtin_ia32_pmovzxbq512_mask ((__v16qi) __A,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -1868,7 +1892,7 @@ _mm512_cvtepu16_epi32 (__m256i __A)
{
return (__m512i) __builtin_ia32_pmovzxwd512_mask ((__v16hi) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -1897,7 +1921,7 @@ _mm512_cvtepu16_epi64 (__m128i __A)
{
return (__m512i) __builtin_ia32_pmovzxwq512_mask ((__v8hi) __A,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -1926,7 +1950,7 @@ _mm512_cvtepu32_epi64 (__m256i __X)
{
return (__m512i) __builtin_ia32_pmovzxdq512_mask ((__v8si) __X,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -1957,7 +1981,7 @@ _mm512_add_round_pd (__m512d __A, __m512d __B, const int __R)
return (__m512d) __builtin_ia32_addpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -1991,7 +2015,7 @@ _mm512_add_round_ps (__m512 __A, __m512 __B, const int __R)
return (__m512) __builtin_ia32_addps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -2024,7 +2048,7 @@ _mm512_sub_round_pd (__m512d __A, __m512d __B, const int __R)
return (__m512d) __builtin_ia32_subpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -2058,7 +2082,7 @@ _mm512_sub_round_ps (__m512 __A, __m512 __B, const int __R)
return (__m512) __builtin_ia32_subps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -2085,7 +2109,7 @@ _mm512_maskz_sub_round_ps (__mmask16 __U, __m512 __A, __m512 __B, const int __R)
}
#else
#define _mm512_add_round_pd(A, B, C) \
- (__m512d)__builtin_ia32_addpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), -1, C)
+ (__m512d)__builtin_ia32_addpd512_mask(A, B, (__v8df)_mm512_undefined_pd(), -1, C)
#define _mm512_mask_add_round_pd(W, U, A, B, C) \
(__m512d)__builtin_ia32_addpd512_mask(A, B, W, U, C)
@@ -2094,7 +2118,7 @@ _mm512_maskz_sub_round_ps (__mmask16 __U, __m512 __A, __m512 __B, const int __R)
(__m512d)__builtin_ia32_addpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), U, C)
#define _mm512_add_round_ps(A, B, C) \
- (__m512)__builtin_ia32_addps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), -1, C)
+ (__m512)__builtin_ia32_addps512_mask(A, B, (__v16sf)_mm512_undefined_ps(), -1, C)
#define _mm512_mask_add_round_ps(W, U, A, B, C) \
(__m512)__builtin_ia32_addps512_mask(A, B, W, U, C)
@@ -2103,7 +2127,7 @@ _mm512_maskz_sub_round_ps (__mmask16 __U, __m512 __A, __m512 __B, const int __R)
(__m512)__builtin_ia32_addps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), U, C)
#define _mm512_sub_round_pd(A, B, C) \
- (__m512d)__builtin_ia32_subpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), -1, C)
+ (__m512d)__builtin_ia32_subpd512_mask(A, B, (__v8df)_mm512_undefined_pd(), -1, C)
#define _mm512_mask_sub_round_pd(W, U, A, B, C) \
(__m512d)__builtin_ia32_subpd512_mask(A, B, W, U, C)
@@ -2112,7 +2136,7 @@ _mm512_maskz_sub_round_ps (__mmask16 __U, __m512 __A, __m512 __B, const int __R)
(__m512d)__builtin_ia32_subpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), U, C)
#define _mm512_sub_round_ps(A, B, C) \
- (__m512)__builtin_ia32_subps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), -1, C)
+ (__m512)__builtin_ia32_subps512_mask(A, B, (__v16sf)_mm512_undefined_ps(), -1, C)
#define _mm512_mask_sub_round_ps(W, U, A, B, C) \
(__m512)__builtin_ia32_subps512_mask(A, B, W, U, C)
@@ -2129,7 +2153,7 @@ _mm512_mul_round_pd (__m512d __A, __m512d __B, const int __R)
return (__m512d) __builtin_ia32_mulpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -2163,7 +2187,7 @@ _mm512_mul_round_ps (__m512 __A, __m512 __B, const int __R)
return (__m512) __builtin_ia32_mulps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -2196,7 +2220,7 @@ _mm512_div_round_pd (__m512d __M, __m512d __V, const int __R)
return (__m512d) __builtin_ia32_divpd512_mask ((__v8df) __M,
(__v8df) __V,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -2230,7 +2254,7 @@ _mm512_div_round_ps (__m512 __A, __m512 __B, const int __R)
return (__m512) __builtin_ia32_divps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -2294,7 +2318,7 @@ _mm_div_round_ss (__m128 __A, __m128 __B, const int __R)
#else
#define _mm512_mul_round_pd(A, B, C) \
- (__m512d)__builtin_ia32_mulpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), -1, C)
+ (__m512d)__builtin_ia32_mulpd512_mask(A, B, (__v8df)_mm512_undefined_pd(), -1, C)
#define _mm512_mask_mul_round_pd(W, U, A, B, C) \
(__m512d)__builtin_ia32_mulpd512_mask(A, B, W, U, C)
@@ -2303,7 +2327,7 @@ _mm_div_round_ss (__m128 __A, __m128 __B, const int __R)
(__m512d)__builtin_ia32_mulpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), U, C)
#define _mm512_mul_round_ps(A, B, C) \
- (__m512)__builtin_ia32_mulps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), -1, C)
+ (__m512)__builtin_ia32_mulps512_mask(A, B, (__v16sf)_mm512_undefined_ps(), -1, C)
#define _mm512_mask_mul_round_ps(W, U, A, B, C) \
(__m512)__builtin_ia32_mulps512_mask(A, B, W, U, C)
@@ -2312,7 +2336,7 @@ _mm_div_round_ss (__m128 __A, __m128 __B, const int __R)
(__m512)__builtin_ia32_mulps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), U, C)
#define _mm512_div_round_pd(A, B, C) \
- (__m512d)__builtin_ia32_divpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), -1, C)
+ (__m512d)__builtin_ia32_divpd512_mask(A, B, (__v8df)_mm512_undefined_pd(), -1, C)
#define _mm512_mask_div_round_pd(W, U, A, B, C) \
(__m512d)__builtin_ia32_divpd512_mask(A, B, W, U, C)
@@ -2321,7 +2345,7 @@ _mm_div_round_ss (__m128 __A, __m128 __B, const int __R)
(__m512d)__builtin_ia32_divpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), U, C)
#define _mm512_div_round_ps(A, B, C) \
- (__m512)__builtin_ia32_divps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), -1, C)
+ (__m512)__builtin_ia32_divps512_mask(A, B, (__v16sf)_mm512_undefined_ps(), -1, C)
#define _mm512_mask_div_round_ps(W, U, A, B, C) \
(__m512)__builtin_ia32_divps512_mask(A, B, W, U, C)
@@ -2350,7 +2374,7 @@ _mm512_max_round_pd (__m512d __A, __m512d __B, const int __R)
return (__m512d) __builtin_ia32_maxpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -2384,7 +2408,7 @@ _mm512_max_round_ps (__m512 __A, __m512 __B, const int __R)
return (__m512) __builtin_ia32_maxps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -2417,7 +2441,7 @@ _mm512_min_round_pd (__m512d __A, __m512d __B, const int __R)
return (__m512d) __builtin_ia32_minpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -2451,7 +2475,7 @@ _mm512_min_round_ps (__m512 __A, __m512 __B, const int __R)
return (__m512) __builtin_ia32_minps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -2478,7 +2502,7 @@ _mm512_maskz_min_round_ps (__mmask16 __U, __m512 __A, __m512 __B, const int __R)
}
#else
#define _mm512_max_round_pd(A, B, R) \
- (__m512d)__builtin_ia32_maxpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), -1, R)
+ (__m512d)__builtin_ia32_maxpd512_mask(A, B, (__v8df)_mm512_undefined_pd(), -1, R)
#define _mm512_mask_max_round_pd(W, U, A, B, R) \
(__m512d)__builtin_ia32_maxpd512_mask(A, B, W, U, R)
@@ -2487,7 +2511,7 @@ _mm512_maskz_min_round_ps (__mmask16 __U, __m512 __A, __m512 __B, const int __R)
(__m512d)__builtin_ia32_maxpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), U, R)
#define _mm512_max_round_ps(A, B, R) \
- (__m512)__builtin_ia32_maxps512_mask(A, B, (__v16sf)_mm512_setzero_pd(), -1, R)
+ (__m512)__builtin_ia32_maxps512_mask(A, B, (__v16sf)_mm512_undefined_pd(), -1, R)
#define _mm512_mask_max_round_ps(W, U, A, B, R) \
(__m512)__builtin_ia32_maxps512_mask(A, B, W, U, R)
@@ -2496,7 +2520,7 @@ _mm512_maskz_min_round_ps (__mmask16 __U, __m512 __A, __m512 __B, const int __R)
(__m512)__builtin_ia32_maxps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), U, R)
#define _mm512_min_round_pd(A, B, R) \
- (__m512d)__builtin_ia32_minpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), -1, R)
+ (__m512d)__builtin_ia32_minpd512_mask(A, B, (__v8df)_mm512_undefined_pd(), -1, R)
#define _mm512_mask_min_round_pd(W, U, A, B, R) \
(__m512d)__builtin_ia32_minpd512_mask(A, B, W, U, R)
@@ -2505,7 +2529,7 @@ _mm512_maskz_min_round_ps (__mmask16 __U, __m512 __A, __m512 __B, const int __R)
(__m512d)__builtin_ia32_minpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), U, R)
#define _mm512_min_round_ps(A, B, R) \
- (__m512)__builtin_ia32_minps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), -1, R)
+ (__m512)__builtin_ia32_minps512_mask(A, B, (__v16sf)_mm512_undefined_ps(), -1, R)
#define _mm512_mask_min_round_ps(W, U, A, B, R) \
(__m512)__builtin_ia32_minps512_mask(A, B, W, U, R)
@@ -2522,7 +2546,7 @@ _mm512_scalef_round_pd (__m512d __A, __m512d __B, const int __R)
return (__m512d) __builtin_ia32_scalefpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -2556,7 +2580,7 @@ _mm512_scalef_round_ps (__m512 __A, __m512 __B, const int __R)
return (__m512) __builtin_ia32_scalefps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -2602,7 +2626,7 @@ _mm_scalef_round_ss (__m128 __A, __m128 __B, const int __R)
}
#else
#define _mm512_scalef_round_pd(A, B, C) \
- (__m512d)__builtin_ia32_scalefpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), -1, C)
+ (__m512d)__builtin_ia32_scalefpd512_mask(A, B, (__v8df)_mm512_undefined_pd(), -1, C)
#define _mm512_mask_scalef_round_pd(W, U, A, B, C) \
(__m512d)__builtin_ia32_scalefpd512_mask(A, B, W, U, C)
@@ -2611,7 +2635,7 @@ _mm_scalef_round_ss (__m128 __A, __m128 __B, const int __R)
(__m512d)__builtin_ia32_scalefpd512_mask(A, B, (__v8df)_mm512_setzero_pd(), U, C)
#define _mm512_scalef_round_ps(A, B, C) \
- (__m512)__builtin_ia32_scalefps512_mask(A, B, (__v16sf)_mm512_setzero_ps(), -1, C)
+ (__m512)__builtin_ia32_scalefps512_mask(A, B, (__v16sf)_mm512_undefined_ps(), -1, C)
#define _mm512_mask_scalef_round_ps(W, U, A, B, C) \
(__m512)__builtin_ia32_scalefps512_mask(A, B, W, U, C)
@@ -3294,7 +3318,7 @@ _mm512_abs_epi64 (__m512i __A)
{
return (__m512i) __builtin_ia32_pabsq512_mask ((__v8di) __A,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -3323,7 +3347,7 @@ _mm512_abs_epi32 (__m512i __A)
{
return (__m512i) __builtin_ia32_pabsd512_mask ((__v16si) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -3350,8 +3374,9 @@ extern __inline __m512
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_broadcastss_ps (__m128 __A)
{
- __v16sf __O;
- return (__m512) __builtin_ia32_broadcastss512 ((__v4sf) __A, __O,
+ return (__m512) __builtin_ia32_broadcastss512 ((__v4sf) __A,
+ (__v16sf)
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -3377,8 +3402,9 @@ extern __inline __m512d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_broadcastsd_pd (__m128d __A)
{
- __v8df __O;
- return (__m512d) __builtin_ia32_broadcastsd512 ((__v2df) __A, __O,
+ return (__m512d) __builtin_ia32_broadcastsd512 ((__v2df) __A,
+ (__v8df)
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -3404,8 +3430,9 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_broadcastd_epi32 (__m128i __A)
{
- __v16si __O;
- return (__m512i) __builtin_ia32_pbroadcastd512 ((__v4si) __A, __O,
+ return (__m512i) __builtin_ia32_pbroadcastd512 ((__v4si) __A,
+ (__v16si)
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -3431,8 +3458,9 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_set1_epi32 (int __A)
{
- __v16si __O;
- return (__m512i) __builtin_ia32_pbroadcastd512_gpr_mask (__A, __O,
+ return (__m512i) __builtin_ia32_pbroadcastd512_gpr_mask (__A,
+ (__v16si)
+ _mm512_undefined_si512 (),
(__mmask16)(-1));
}
@@ -3458,8 +3486,9 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_broadcastq_epi64 (__m128i __A)
{
- __v8di __O;
- return (__m512i) __builtin_ia32_pbroadcastq512 ((__v2di) __A, __O,
+ return (__m512i) __builtin_ia32_pbroadcastq512 ((__v2di) __A,
+ (__v8di)
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -3485,12 +3514,15 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_set1_epi64 (long long __A)
{
- __v8di __O;
#ifdef TARGET_64BIT
- return (__m512i) __builtin_ia32_pbroadcastq512_gpr_mask (__A, __O,
+ return (__m512i) __builtin_ia32_pbroadcastq512_gpr_mask (__A,
+ (__v8di)
+ _mm512_undefined_si512 (),
(__mmask8)(-1));
#else
- return (__m512i) __builtin_ia32_pbroadcastq512_mem_mask (__A, __O,
+ return (__m512i) __builtin_ia32_pbroadcastq512_mem_mask (__A,
+ (__v8di)
+ _mm512_undefined_si512 (),
(__mmask8)(-1));
#endif
}
@@ -3529,8 +3561,9 @@ extern __inline __m512
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_broadcast_f32x4 (__m128 __A)
{
- __v16sf __O;
- return (__m512) __builtin_ia32_broadcastf32x4_512 ((__v4sf) __A, __O,
+ return (__m512) __builtin_ia32_broadcastf32x4_512 ((__v4sf) __A,
+ (__v16sf)
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -3557,9 +3590,9 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_broadcast_i32x4 (__m128i __A)
{
- __v16si __O;
return (__m512i) __builtin_ia32_broadcasti32x4_512 ((__v4si) __A,
- __O,
+ (__v16si)
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -3586,9 +3619,9 @@ extern __inline __m512d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_broadcast_f64x4 (__m256d __A)
{
- __v8df __O;
return (__m512d) __builtin_ia32_broadcastf64x4_512 ((__v4df) __A,
- __O,
+ (__v8df)
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -3615,9 +3648,9 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_broadcast_i64x4 (__m256i __A)
{
- __v8di __O;
return (__m512i) __builtin_ia32_broadcasti64x4_512 ((__v4di) __A,
- __O,
+ (__v8di)
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -3738,7 +3771,7 @@ _mm512_shuffle_epi32 (__m512i __A, _MM_PERM_ENUM __mask)
return (__m512i) __builtin_ia32_pshufd512_mask ((__v16si) __A,
__mask,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -3771,7 +3804,7 @@ _mm512_shuffle_i64x2 (__m512i __A, __m512i __B, const int __imm)
return (__m512i) __builtin_ia32_shuf_i64x2_mask ((__v8di) __A,
(__v8di) __B, __imm,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -3806,7 +3839,7 @@ _mm512_shuffle_i32x4 (__m512i __A, __m512i __B, const int __imm)
(__v16si) __B,
__imm,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -3842,7 +3875,7 @@ _mm512_shuffle_f64x2 (__m512d __A, __m512d __B, const int __imm)
return (__m512d) __builtin_ia32_shuf_f64x2_mask ((__v8df) __A,
(__v8df) __B, __imm,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -3876,7 +3909,7 @@ _mm512_shuffle_f32x4 (__m512 __A, __m512 __B, const int __imm)
return (__m512) __builtin_ia32_shuf_f32x4_mask ((__v16sf) __A,
(__v16sf) __B, __imm,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -3906,7 +3939,7 @@ _mm512_maskz_shuffle_f32x4 (__mmask16 __U, __m512 __A, __m512 __B,
#else
#define _mm512_shuffle_epi32(X, C) \
((__m512i) __builtin_ia32_pshufd512_mask ((__v16si)(__m512i)(X), (int)(C),\
- (__v16si)(__m512i)_mm512_setzero_si512 (),\
+ (__v16si)(__m512i)_mm512_undefined_si512 (),\
(__mmask16)-1))
#define _mm512_mask_shuffle_epi32(W, U, X, C) \
@@ -3922,7 +3955,7 @@ _mm512_maskz_shuffle_f32x4 (__mmask16 __U, __m512 __A, __m512 __B,
#define _mm512_shuffle_i64x2(X, Y, C) \
((__m512i) __builtin_ia32_shuf_i64x2_mask ((__v8di)(__m512i)(X), \
(__v8di)(__m512i)(Y), (int)(C),\
- (__v8di)(__m512i)_mm512_setzero_si512 (),\
+ (__v8di)(__m512i)_mm512_undefined_si512 (),\
(__mmask8)-1))
#define _mm512_mask_shuffle_i64x2(W, U, X, Y, C) \
@@ -3940,7 +3973,7 @@ _mm512_maskz_shuffle_f32x4 (__mmask16 __U, __m512 __A, __m512 __B,
#define _mm512_shuffle_i32x4(X, Y, C) \
((__m512i) __builtin_ia32_shuf_i32x4_mask ((__v16si)(__m512i)(X), \
(__v16si)(__m512i)(Y), (int)(C),\
- (__v16si)(__m512i)_mm512_setzero_si512 (),\
+ (__v16si)(__m512i)_mm512_undefined_si512 (),\
(__mmask16)-1))
#define _mm512_mask_shuffle_i32x4(W, U, X, Y, C) \
@@ -3958,7 +3991,7 @@ _mm512_maskz_shuffle_f32x4 (__mmask16 __U, __m512 __A, __m512 __B,
#define _mm512_shuffle_f64x2(X, Y, C) \
((__m512d) __builtin_ia32_shuf_f64x2_mask ((__v8df)(__m512d)(X), \
(__v8df)(__m512d)(Y), (int)(C),\
- (__v8df)(__m512d)_mm512_setzero_pd(),\
+ (__v8df)(__m512d)_mm512_undefined_pd(),\
(__mmask8)-1))
#define _mm512_mask_shuffle_f64x2(W, U, X, Y, C) \
@@ -3976,7 +4009,7 @@ _mm512_maskz_shuffle_f32x4 (__mmask16 __U, __m512 __A, __m512 __B,
#define _mm512_shuffle_f32x4(X, Y, C) \
((__m512) __builtin_ia32_shuf_f32x4_mask ((__v16sf)(__m512)(X), \
(__v16sf)(__m512)(Y), (int)(C),\
- (__v16sf)(__m512)_mm512_setzero_ps(),\
+ (__v16sf)(__m512)_mm512_undefined_ps(),\
(__mmask16)-1))
#define _mm512_mask_shuffle_f32x4(W, U, X, Y, C) \
@@ -3999,7 +4032,7 @@ _mm512_rolv_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_prolvd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -4031,7 +4064,7 @@ _mm512_rorv_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_prorvd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -4063,7 +4096,7 @@ _mm512_rolv_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_prolvq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -4095,7 +4128,7 @@ _mm512_rorv_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_prorvq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -4127,7 +4160,7 @@ _mm512_cvtt_roundpd_epi32 (__m512d __A, const int __R)
{
return (__m256i) __builtin_ia32_cvttpd2dq512_mask ((__v8df) __A,
(__v8si)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1, __R);
}
@@ -4157,7 +4190,7 @@ _mm512_cvtt_roundpd_epu32 (__m512d __A, const int __R)
{
return (__m256i) __builtin_ia32_cvttpd2udq512_mask ((__v8df) __A,
(__v8si)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1, __R);
}
@@ -4182,7 +4215,7 @@ _mm512_maskz_cvtt_roundpd_epu32 (__mmask8 __U, __m512d __A, const int __R)
}
#else
#define _mm512_cvtt_roundpd_epi32(A, B) \
- ((__m256i)__builtin_ia32_cvttpd2dq512_mask(A, (__v8si)_mm256_setzero_si256(), -1, B))
+ ((__m256i)__builtin_ia32_cvttpd2dq512_mask(A, (__v8si)_mm256_undefined_si256(), -1, B))
#define _mm512_mask_cvtt_roundpd_epi32(W, U, A, B) \
((__m256i)__builtin_ia32_cvttpd2dq512_mask(A, (__v8si)(W), U, B))
@@ -4191,7 +4224,7 @@ _mm512_maskz_cvtt_roundpd_epu32 (__mmask8 __U, __m512d __A, const int __R)
((__m256i)__builtin_ia32_cvttpd2dq512_mask(A, (__v8si)_mm256_setzero_si256(), U, B))
#define _mm512_cvtt_roundpd_epu32(A, B) \
- ((__m256i)__builtin_ia32_cvttpd2udq512_mask(A, (__v8si)_mm256_setzero_si256(), -1, B))
+ ((__m256i)__builtin_ia32_cvttpd2udq512_mask(A, (__v8si)_mm256_undefined_si256(), -1, B))
#define _mm512_mask_cvtt_roundpd_epu32(W, U, A, B) \
((__m256i)__builtin_ia32_cvttpd2udq512_mask(A, (__v8si)(W), U, B))
@@ -4207,7 +4240,7 @@ _mm512_cvt_roundpd_epi32 (__m512d __A, const int __R)
{
return (__m256i) __builtin_ia32_cvtpd2dq512_mask ((__v8df) __A,
(__v8si)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1, __R);
}
@@ -4237,7 +4270,7 @@ _mm512_cvt_roundpd_epu32 (__m512d __A, const int __R)
{
return (__m256i) __builtin_ia32_cvtpd2udq512_mask ((__v8df) __A,
(__v8si)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1, __R);
}
@@ -4262,7 +4295,7 @@ _mm512_maskz_cvt_roundpd_epu32 (__mmask8 __U, __m512d __A, const int __R)
}
#else
#define _mm512_cvt_roundpd_epi32(A, B) \
- ((__m256i)__builtin_ia32_cvtpd2dq512_mask(A, (__v8si)_mm256_setzero_si256(), -1, B))
+ ((__m256i)__builtin_ia32_cvtpd2dq512_mask(A, (__v8si)_mm256_undefined_si256(), -1, B))
#define _mm512_mask_cvt_roundpd_epi32(W, U, A, B) \
((__m256i)__builtin_ia32_cvtpd2dq512_mask(A, (__v8si)(W), U, B))
@@ -4271,7 +4304,7 @@ _mm512_maskz_cvt_roundpd_epu32 (__mmask8 __U, __m512d __A, const int __R)
((__m256i)__builtin_ia32_cvtpd2dq512_mask(A, (__v8si)_mm256_setzero_si256(), U, B))
#define _mm512_cvt_roundpd_epu32(A, B) \
- ((__m256i)__builtin_ia32_cvtpd2udq512_mask(A, (__v8si)_mm256_setzero_si256(), -1, B))
+ ((__m256i)__builtin_ia32_cvtpd2udq512_mask(A, (__v8si)_mm256_undefined_si256(), -1, B))
#define _mm512_mask_cvt_roundpd_epu32(W, U, A, B) \
((__m256i)__builtin_ia32_cvtpd2udq512_mask(A, (__v8si)(W), U, B))
@@ -4287,7 +4320,7 @@ _mm512_cvtt_roundps_epi32 (__m512 __A, const int __R)
{
return (__m512i) __builtin_ia32_cvttps2dq512_mask ((__v16sf) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1, __R);
}
@@ -4317,7 +4350,7 @@ _mm512_cvtt_roundps_epu32 (__m512 __A, const int __R)
{
return (__m512i) __builtin_ia32_cvttps2udq512_mask ((__v16sf) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1, __R);
}
@@ -4342,7 +4375,7 @@ _mm512_maskz_cvtt_roundps_epu32 (__mmask16 __U, __m512 __A, const int __R)
}
#else
#define _mm512_cvtt_roundps_epi32(A, B) \
- ((__m512i)__builtin_ia32_cvttps2dq512_mask(A, (__v16si)_mm512_setzero_si512 (), -1, B))
+ ((__m512i)__builtin_ia32_cvttps2dq512_mask(A, (__v16si)_mm512_undefined_si512 (), -1, B))
#define _mm512_mask_cvtt_roundps_epi32(W, U, A, B) \
((__m512i)__builtin_ia32_cvttps2dq512_mask(A, (__v16si)(W), U, B))
@@ -4351,7 +4384,7 @@ _mm512_maskz_cvtt_roundps_epu32 (__mmask16 __U, __m512 __A, const int __R)
((__m512i)__builtin_ia32_cvttps2dq512_mask(A, (__v16si)_mm512_setzero_si512 (), U, B))
#define _mm512_cvtt_roundps_epu32(A, B) \
- ((__m512i)__builtin_ia32_cvttps2udq512_mask(A, (__v16si)_mm512_setzero_si512 (), -1, B))
+ ((__m512i)__builtin_ia32_cvttps2udq512_mask(A, (__v16si)_mm512_undefined_si512 (), -1, B))
#define _mm512_mask_cvtt_roundps_epu32(W, U, A, B) \
((__m512i)__builtin_ia32_cvttps2udq512_mask(A, (__v16si)(W), U, B))
@@ -4367,7 +4400,7 @@ _mm512_cvt_roundps_epi32 (__m512 __A, const int __R)
{
return (__m512i) __builtin_ia32_cvtps2dq512_mask ((__v16sf) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1, __R);
}
@@ -4397,7 +4430,7 @@ _mm512_cvt_roundps_epu32 (__m512 __A, const int __R)
{
return (__m512i) __builtin_ia32_cvtps2udq512_mask ((__v16sf) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1, __R);
}
@@ -4422,7 +4455,7 @@ _mm512_maskz_cvt_roundps_epu32 (__mmask16 __U, __m512 __A, const int __R)
}
#else
#define _mm512_cvt_roundps_epi32(A, B) \
- ((__m512i)__builtin_ia32_cvtps2dq512_mask(A, (__v16si)_mm512_setzero_si512 (), -1, B))
+ ((__m512i)__builtin_ia32_cvtps2dq512_mask(A, (__v16si)_mm512_undefined_si512 (), -1, B))
#define _mm512_mask_cvt_roundps_epi32(W, U, A, B) \
((__m512i)__builtin_ia32_cvtps2dq512_mask(A, (__v16si)(W), U, B))
@@ -4431,7 +4464,7 @@ _mm512_maskz_cvt_roundps_epu32 (__mmask16 __U, __m512 __A, const int __R)
((__m512i)__builtin_ia32_cvtps2dq512_mask(A, (__v16si)_mm512_setzero_si512 (), U, B))
#define _mm512_cvt_roundps_epu32(A, B) \
- ((__m512i)__builtin_ia32_cvtps2udq512_mask(A, (__v16si)_mm512_setzero_si512 (), -1, B))
+ ((__m512i)__builtin_ia32_cvtps2udq512_mask(A, (__v16si)_mm512_undefined_si512 (), -1, B))
#define _mm512_mask_cvt_roundps_epu32(W, U, A, B) \
((__m512i)__builtin_ia32_cvtps2udq512_mask(A, (__v16si)(W), U, B))
@@ -4553,8 +4586,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtepi32_epi8 (__m512i __A)
{
- __v16qi __O;
- return (__m128i) __builtin_ia32_pmovdb512_mask ((__v16si) __A, __O,
+ return (__m128i) __builtin_ia32_pmovdb512_mask ((__v16si) __A,
+ (__v16qi)
+ _mm_undefined_si128 (),
(__mmask16) -1);
}
@@ -4587,8 +4621,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtsepi32_epi8 (__m512i __A)
{
- __v16qi __O;
- return (__m128i) __builtin_ia32_pmovsdb512_mask ((__v16si) __A, __O,
+ return (__m128i) __builtin_ia32_pmovsdb512_mask ((__v16si) __A,
+ (__v16qi)
+ _mm_undefined_si128 (),
(__mmask16) -1);
}
@@ -4621,8 +4656,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtusepi32_epi8 (__m512i __A)
{
- __v16qi __O;
- return (__m128i) __builtin_ia32_pmovusdb512_mask ((__v16si) __A, __O,
+ return (__m128i) __builtin_ia32_pmovusdb512_mask ((__v16si) __A,
+ (__v16qi)
+ _mm_undefined_si128 (),
(__mmask16) -1);
}
@@ -4656,8 +4692,9 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtepi32_epi16 (__m512i __A)
{
- __v16hi __O;
- return (__m256i) __builtin_ia32_pmovdw512_mask ((__v16si) __A, __O,
+ return (__m256i) __builtin_ia32_pmovdw512_mask ((__v16si) __A,
+ (__v16hi)
+ _mm256_undefined_si256 (),
(__mmask16) -1);
}
@@ -4690,8 +4727,9 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtsepi32_epi16 (__m512i __A)
{
- __v16hi __O;
- return (__m256i) __builtin_ia32_pmovsdw512_mask ((__v16si) __A, __O,
+ return (__m256i) __builtin_ia32_pmovsdw512_mask ((__v16si) __A,
+ (__v16hi)
+ _mm256_undefined_si256 (),
(__mmask16) -1);
}
@@ -4724,8 +4762,9 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtusepi32_epi16 (__m512i __A)
{
- __v16hi __O;
- return (__m256i) __builtin_ia32_pmovusdw512_mask ((__v16si) __A, __O,
+ return (__m256i) __builtin_ia32_pmovusdw512_mask ((__v16si) __A,
+ (__v16hi)
+ _mm256_undefined_si256 (),
(__mmask16) -1);
}
@@ -4759,8 +4798,9 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtepi64_epi32 (__m512i __A)
{
- __v8si __O;
- return (__m256i) __builtin_ia32_pmovqd512_mask ((__v8di) __A, __O,
+ return (__m256i) __builtin_ia32_pmovqd512_mask ((__v8di) __A,
+ (__v8si)
+ _mm256_undefined_si256 (),
(__mmask8) -1);
}
@@ -4794,7 +4834,9 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtsepi64_epi32 (__m512i __A)
{
__v8si __O;
- return (__m256i) __builtin_ia32_pmovsqd512_mask ((__v8di) __A, __O,
+ return (__m256i) __builtin_ia32_pmovsqd512_mask ((__v8di) __A,
+ (__v8si)
+ _mm256_undefined_si256 (),
(__mmask8) -1);
}
@@ -4827,8 +4869,9 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtusepi64_epi32 (__m512i __A)
{
- __v8si __O;
- return (__m256i) __builtin_ia32_pmovusqd512_mask ((__v8di) __A, __O,
+ return (__m256i) __builtin_ia32_pmovusqd512_mask ((__v8di) __A,
+ (__v8si)
+ _mm256_undefined_si256 (),
(__mmask8) -1);
}
@@ -4861,8 +4904,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtepi64_epi16 (__m512i __A)
{
- __v8hi __O;
- return (__m128i) __builtin_ia32_pmovqw512_mask ((__v8di) __A, __O,
+ return (__m128i) __builtin_ia32_pmovqw512_mask ((__v8di) __A,
+ (__v8hi)
+ _mm_undefined_si128 (),
(__mmask8) -1);
}
@@ -4895,8 +4939,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtsepi64_epi16 (__m512i __A)
{
- __v8hi __O;
- return (__m128i) __builtin_ia32_pmovsqw512_mask ((__v8di) __A, __O,
+ return (__m128i) __builtin_ia32_pmovsqw512_mask ((__v8di) __A,
+ (__v8hi)
+ _mm_undefined_si128 (),
(__mmask8) -1);
}
@@ -4929,8 +4974,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtusepi64_epi16 (__m512i __A)
{
- __v8hi __O;
- return (__m128i) __builtin_ia32_pmovusqw512_mask ((__v8di) __A, __O,
+ return (__m128i) __builtin_ia32_pmovusqw512_mask ((__v8di) __A,
+ (__v8hi)
+ _mm_undefined_si128 (),
(__mmask8) -1);
}
@@ -4963,8 +5009,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtepi64_epi8 (__m512i __A)
{
- __v16qi __O;
- return (__m128i) __builtin_ia32_pmovqb512_mask ((__v8di) __A, __O,
+ return (__m128i) __builtin_ia32_pmovqb512_mask ((__v8di) __A,
+ (__v16qi)
+ _mm_undefined_si128 (),
(__mmask8) -1);
}
@@ -4997,8 +5044,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtsepi64_epi8 (__m512i __A)
{
- __v16qi __O;
- return (__m128i) __builtin_ia32_pmovsqb512_mask ((__v8di) __A, __O,
+ return (__m128i) __builtin_ia32_pmovsqb512_mask ((__v8di) __A,
+ (__v16qi)
+ _mm_undefined_si128 (),
(__mmask8) -1);
}
@@ -5031,8 +5079,9 @@ extern __inline __m128i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_cvtusepi64_epi8 (__m512i __A)
{
- __v16qi __O;
- return (__m128i) __builtin_ia32_pmovusqb512_mask ((__v8di) __A, __O,
+ return (__m128i) __builtin_ia32_pmovusqb512_mask ((__v8di) __A,
+ (__v16qi)
+ _mm_undefined_si128 (),
(__mmask8) -1);
}
@@ -5068,7 +5117,7 @@ _mm512_cvtepi32_pd (__m256i __A)
{
return (__m512d) __builtin_ia32_cvtdq2pd512_mask ((__v8si) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -5097,7 +5146,7 @@ _mm512_cvtepu32_pd (__m256i __A)
{
return (__m512d) __builtin_ia32_cvtudq2pd512_mask ((__v8si) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -5127,7 +5176,7 @@ _mm512_cvt_roundepi32_ps (__m512i __A, const int __R)
{
return (__m512) __builtin_ia32_cvtdq2ps512_mask ((__v16si) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -5157,7 +5206,7 @@ _mm512_cvt_roundepu32_ps (__m512i __A, const int __R)
{
return (__m512) __builtin_ia32_cvtudq2ps512_mask ((__v16si) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -5183,7 +5232,7 @@ _mm512_maskz_cvt_roundepu32_ps (__mmask16 __U, __m512i __A, const int __R)
#else
#define _mm512_cvt_roundepi32_ps(A, B) \
- (__m512)__builtin_ia32_cvtdq2ps512_mask((__v16si)(A), (__v16sf)_mm512_setzero_ps(), -1, B)
+ (__m512)__builtin_ia32_cvtdq2ps512_mask((__v16si)(A), (__v16sf)_mm512_undefined_ps(), -1, B)
#define _mm512_mask_cvt_roundepi32_ps(W, U, A, B) \
(__m512)__builtin_ia32_cvtdq2ps512_mask((__v16si)(A), W, U, B)
@@ -5192,7 +5241,7 @@ _mm512_maskz_cvt_roundepu32_ps (__mmask16 __U, __m512i __A, const int __R)
(__m512)__builtin_ia32_cvtdq2ps512_mask((__v16si)(A), (__v16sf)_mm512_setzero_ps(), U, B)
#define _mm512_cvt_roundepu32_ps(A, B) \
- (__m512)__builtin_ia32_cvtudq2ps512_mask((__v16si)(A), (__v16sf)_mm512_setzero_ps(), -1, B)
+ (__m512)__builtin_ia32_cvtudq2ps512_mask((__v16si)(A), (__v16sf)_mm512_undefined_ps(), -1, B)
#define _mm512_mask_cvt_roundepu32_ps(W, U, A, B) \
(__m512)__builtin_ia32_cvtudq2ps512_mask((__v16si)(A), W, U, B)
@@ -5209,7 +5258,7 @@ _mm512_extractf64x4_pd (__m512d __A, const int __imm)
return (__m256d) __builtin_ia32_extractf64x4_mask ((__v8df) __A,
__imm,
(__v4df)
- _mm256_setzero_pd (),
+ _mm256_undefined_pd (),
(__mmask8) -1);
}
@@ -5242,7 +5291,7 @@ _mm512_extractf32x4_ps (__m512 __A, const int __imm)
return (__m128) __builtin_ia32_extractf32x4_mask ((__v16sf) __A,
__imm,
(__v4sf)
- _mm_setzero_ps (),
+ _mm_undefined_ps (),
(__mmask8) -1);
}
@@ -5275,7 +5324,7 @@ _mm512_extracti64x4_epi64 (__m512i __A, const int __imm)
return (__m256i) __builtin_ia32_extracti64x4_mask ((__v8di) __A,
__imm,
(__v4di)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1);
}
@@ -5308,7 +5357,7 @@ _mm512_extracti32x4_epi32 (__m512i __A, const int __imm)
return (__m128i) __builtin_ia32_extracti32x4_mask ((__v16si) __A,
__imm,
(__v4si)
- _mm_setzero_si128 (),
+ _mm_undefined_si128 (),
(__mmask8) -1);
}
@@ -5338,7 +5387,7 @@ _mm512_maskz_extracti32x4_epi32 (__mmask8 __U, __m512i __A, const int __imm)
#define _mm512_extractf64x4_pd(X, C) \
((__m256d) __builtin_ia32_extractf64x4_mask ((__v8df)(__m512d) (X), \
(int) (C),\
- (__v4df)(__m256d)_mm256_setzero_pd(),\
+ (__v4df)(__m256d)_mm256_undefined_pd(),\
(__mmask8)-1))
#define _mm512_mask_extractf64x4_pd(W, U, X, C) \
@@ -5356,7 +5405,7 @@ _mm512_maskz_extracti32x4_epi32 (__mmask8 __U, __m512i __A, const int __imm)
#define _mm512_extractf32x4_ps(X, C) \
((__m128) __builtin_ia32_extractf32x4_mask ((__v16sf)(__m512) (X), \
(int) (C),\
- (__v4sf)(__m128)_mm_setzero_ps(),\
+ (__v4sf)(__m128)_mm_undefined_ps(),\
(__mmask8)-1))
#define _mm512_mask_extractf32x4_ps(W, U, X, C) \
@@ -5374,7 +5423,7 @@ _mm512_maskz_extracti32x4_epi32 (__mmask8 __U, __m512i __A, const int __imm)
#define _mm512_extracti64x4_epi64(X, C) \
((__m256i) __builtin_ia32_extracti64x4_mask ((__v8di)(__m512i) (X), \
(int) (C),\
- (__v4di)(__m256i)_mm256_setzero_si256 (),\
+ (__v4di)(__m256i)_mm256_undefined_si256 (),\
(__mmask8)-1))
#define _mm512_mask_extracti64x4_epi64(W, U, X, C) \
@@ -5392,7 +5441,7 @@ _mm512_maskz_extracti32x4_epi32 (__mmask8 __U, __m512i __A, const int __imm)
#define _mm512_extracti32x4_epi32(X, C) \
((__m128i) __builtin_ia32_extracti32x4_mask ((__v16si)(__m512i) (X), \
(int) (C),\
- (__v4si)(__m128i)_mm_setzero_si128 (),\
+ (__v4si)(__m128i)_mm_undefined_si128 (),\
(__mmask8)-1))
#define _mm512_mask_extracti32x4_epi32(W, U, X, C) \
@@ -5437,7 +5486,7 @@ _mm512_inserti64x4 (__m512i __A, __m256i __B, const int __imm)
(__v4di) __B,
__imm,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -5474,7 +5523,7 @@ _mm512_insertf64x4 (__m512d __A, __m256d __B, const int __imm)
(__v4df) __B,
__imm,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -5514,7 +5563,7 @@ _mm512_maskz_insertf64x4 (__mmask8 __U, __m512d __A, __m256d __B,
#define _mm512_insertf64x4(X, Y, C) \
((__m512d) __builtin_ia32_insertf64x4_mask ((__v8df)(__m512d) (X), \
(__v4df)(__m256d) (Y), (int) (C), \
- (__v8df)(__m512d)_mm512_setzero_pd(), \
+ (__v8df)(__m512d)_mm512_undefined_pd(), \
(__mmask8)-1))
#define _mm512_mask_insertf64x4(W, U, X, Y, C) \
@@ -5532,7 +5581,7 @@ _mm512_maskz_insertf64x4 (__mmask8 __U, __m512d __A, __m256d __B,
#define _mm512_inserti64x4(X, Y, C) \
((__m512i) __builtin_ia32_inserti64x4_mask ((__v8di)(__m512i) (X), \
(__v4di)(__m256i) (Y), (int) (C), \
- (__v8di)(__m512i)_mm512_setzero_si512 (), \
+ (__v8di)(__m512i)_mm512_undefined_si512 (), \
(__mmask8)-1))
#define _mm512_mask_inserti64x4(W, U, X, Y, C) \
@@ -5554,7 +5603,7 @@ _mm512_loadu_pd (void const *__P)
{
return (__m512d) __builtin_ia32_loadupd512_mask ((const __v8df *) __P,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -5599,7 +5648,7 @@ _mm512_loadu_ps (void const *__P)
{
return (__m512) __builtin_ia32_loadups512_mask ((const __v16sf *) __P,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -5717,7 +5766,7 @@ _mm512_permutevar_pd (__m512d __A, __m512i __C)
return (__m512d) __builtin_ia32_vpermilvarpd512_mask ((__v8df) __A,
(__v8di) __C,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -5749,7 +5798,7 @@ _mm512_permutevar_ps (__m512 __A, __m512i __C)
return (__m512) __builtin_ia32_vpermilvarps512_mask ((__v16sf) __A,
(__v16si) __C,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -5968,7 +6017,7 @@ _mm512_permute_pd (__m512d __X, const int __C)
{
return (__m512d) __builtin_ia32_vpermilpd512_mask ((__v8df) __X, __C,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -5997,7 +6046,7 @@ _mm512_permute_ps (__m512 __X, const int __C)
{
return (__m512) __builtin_ia32_vpermilps512_mask ((__v16sf) __X, __C,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -6022,7 +6071,7 @@ _mm512_maskz_permute_ps (__mmask16 __U, __m512 __X, const int __C)
#else
#define _mm512_permute_pd(X, C) \
((__m512d) __builtin_ia32_vpermilpd512_mask ((__v8df)(__m512d)(X), (int)(C), \
- (__v8df)(__m512d)(X), \
+ (__v8df)(__m512d)_mm512_undefined_pd(),\
(__mmask8)(-1)))
#define _mm512_mask_permute_pd(W, U, X, C) \
@@ -6037,7 +6086,7 @@ _mm512_maskz_permute_ps (__mmask16 __U, __m512 __X, const int __C)
#define _mm512_permute_ps(X, C) \
((__m512) __builtin_ia32_vpermilps512_mask ((__v16sf)(__m512)(X), (int)(C), \
- (__v16sf)(__m512)(X), \
+ (__v16sf)(__m512)_mm512_undefined_ps(),\
(__mmask16)(-1)))
#define _mm512_mask_permute_ps(W, U, X, C) \
@@ -6058,7 +6107,7 @@ _mm512_permutex_epi64 (__m512i __X, const int __I)
{
return (__m512i) __builtin_ia32_permdi512_mask ((__v8di) __X, __I,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) (-1));
}
@@ -6088,7 +6137,7 @@ _mm512_permutex_pd (__m512d __X, const int __M)
{
return (__m512d) __builtin_ia32_permdf512_mask ((__v8df) __X, __M,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -6113,7 +6162,8 @@ _mm512_maskz_permutex_pd (__mmask8 __U, __m512d __X, const int __M)
#else
#define _mm512_permutex_pd(X, M) \
((__m512d) __builtin_ia32_permdf512_mask ((__v8df)(__m512d)(X), (int)(M), \
- (__v8df)(__m512d)(X), (__mmask8)-1))
+ (__v8df)(__m512d)_mm512_undefined_pd(),\
+ (__mmask8)-1))
#define _mm512_mask_permutex_pd(W, U, X, M) \
((__m512d) __builtin_ia32_permdf512_mask ((__v8df)(__m512d)(X), (int)(M), \
@@ -6127,7 +6177,8 @@ _mm512_maskz_permutex_pd (__mmask8 __U, __m512d __X, const int __M)
#define _mm512_permutex_epi64(X, I) \
((__m512i) __builtin_ia32_permdi512_mask ((__v8di)(__m512i)(X), \
(int)(I), \
- (__v8di)(__m512i)(X), \
+ (__v8di)(__m512i) \
+ (_mm512_undefined_si512 ()),\
(__mmask8)(-1)))
#define _mm512_maskz_permutex_epi64(M, X, I) \
@@ -6162,7 +6213,7 @@ _mm512_permutexvar_epi64 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_permvardi512_mask ((__v8di) __Y,
(__v8di) __X,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -6195,7 +6246,7 @@ _mm512_permutexvar_epi32 (__m512i __X, __m512i __Y)
return (__m512i) __builtin_ia32_permvarsi512_mask ((__v16si) __Y,
(__v16si) __X,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -6217,7 +6268,7 @@ _mm512_permutexvar_pd (__m512i __X, __m512d __Y)
return (__m512d) __builtin_ia32_permvardf512_mask ((__v8df) __Y,
(__v8di) __X,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -6249,7 +6300,7 @@ _mm512_permutexvar_ps (__m512i __X, __m512 __Y)
return (__m512) __builtin_ia32_permvarsf512_mask ((__v16sf) __Y,
(__v16si) __X,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -6282,7 +6333,7 @@ _mm512_shuffle_ps (__m512 __M, __m512 __V, const int __imm)
return (__m512) __builtin_ia32_shufps512_mask ((__v16sf) __M,
(__v16sf) __V, __imm,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -6315,7 +6366,7 @@ _mm512_shuffle_pd (__m512d __M, __m512d __V, const int __imm)
return (__m512d) __builtin_ia32_shufpd512_mask ((__v8df) __M,
(__v8df) __V, __imm,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -6485,7 +6536,7 @@ _mm_maskz_fixupimm_round_ss (__mmask8 __U, __m128 __A, __m128 __B,
#define _mm512_shuffle_pd(X, Y, C) \
((__m512d)__builtin_ia32_shufpd512_mask ((__v8df)(__m512d)(X), \
(__v8df)(__m512d)(Y), (int)(C),\
- (__v8df)(__m512d)_mm512_setzero_pd(),\
+ (__v8df)(__m512d)_mm512_undefined_pd(),\
(__mmask8)-1))
#define _mm512_mask_shuffle_pd(W, U, X, Y, C) \
@@ -6503,7 +6554,7 @@ _mm_maskz_fixupimm_round_ss (__mmask8 __U, __m128 __A, __m128 __B,
#define _mm512_shuffle_ps(X, Y, C) \
((__m512)__builtin_ia32_shufps512_mask ((__v16sf)(__m512)(X), \
(__v16sf)(__m512)(Y), (int)(C),\
- (__v16sf)(__m512)_mm512_setzero_ps(),\
+ (__v16sf)(__m512)_mm512_undefined_ps(),\
(__mmask16)-1))
#define _mm512_mask_shuffle_ps(W, U, X, Y, C) \
@@ -6585,7 +6636,7 @@ _mm512_movehdup_ps (__m512 __A)
{
return (__m512) __builtin_ia32_movshdup512_mask ((__v16sf) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -6614,7 +6665,7 @@ _mm512_moveldup_ps (__m512 __A)
{
return (__m512) __builtin_ia32_movsldup512_mask ((__v16sf) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -6644,7 +6695,7 @@ _mm512_or_si512 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pord512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -6655,7 +6706,7 @@ _mm512_or_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pord512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -6687,7 +6738,7 @@ _mm512_or_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_porq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -6719,7 +6770,7 @@ _mm512_xor_si512 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pxord512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -6730,7 +6781,7 @@ _mm512_xor_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pxord512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -6762,7 +6813,7 @@ _mm512_xor_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pxorq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -6794,7 +6845,7 @@ _mm512_rol_epi32 (__m512i __A, const int __B)
{
return (__m512i) __builtin_ia32_prold512_mask ((__v16si) __A, __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -6823,7 +6874,7 @@ _mm512_ror_epi32 (__m512i __A, int __B)
{
return (__m512i) __builtin_ia32_prord512_mask ((__v16si) __A, __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -6852,7 +6903,7 @@ _mm512_rol_epi64 (__m512i __A, const int __B)
{
return (__m512i) __builtin_ia32_prolq512_mask ((__v8di) __A, __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -6881,7 +6932,7 @@ _mm512_ror_epi64 (__m512i __A, int __B)
{
return (__m512i) __builtin_ia32_prorq512_mask ((__v8di) __A, __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -6908,7 +6959,7 @@ _mm512_maskz_ror_epi64 (__mmask8 __U, __m512i __A, int __B)
#define _mm512_rol_epi32(A, B) \
((__m512i)__builtin_ia32_prold512_mask ((__v16si)(__m512i)(A), \
(int)(B), \
- (__v16si)_mm512_setzero_si512 (), \
+ (__v16si)_mm512_undefined_si512 (), \
(__mmask16)(-1)))
#define _mm512_mask_rol_epi32(W, U, A, B) \
((__m512i)__builtin_ia32_prold512_mask ((__v16si)(__m512i)(A), \
@@ -6923,7 +6974,7 @@ _mm512_maskz_ror_epi64 (__mmask8 __U, __m512i __A, int __B)
#define _mm512_ror_epi32(A, B) \
((__m512i)__builtin_ia32_prord512_mask ((__v16si)(__m512i)(A), \
(int)(B), \
- (__v16si)_mm512_setzero_si512 (), \
+ (__v16si)_mm512_undefined_si512 (), \
(__mmask16)(-1)))
#define _mm512_mask_ror_epi32(W, U, A, B) \
((__m512i)__builtin_ia32_prord512_mask ((__v16si)(__m512i)(A), \
@@ -6938,7 +6989,7 @@ _mm512_maskz_ror_epi64 (__mmask8 __U, __m512i __A, int __B)
#define _mm512_rol_epi64(A, B) \
((__m512i)__builtin_ia32_prolq512_mask ((__v8di)(__m512i)(A), \
(int)(B), \
- (__v8di)_mm512_setzero_si512 (), \
+ (__v8di)_mm512_undefined_si512 (), \
(__mmask8)(-1)))
#define _mm512_mask_rol_epi64(W, U, A, B) \
((__m512i)__builtin_ia32_prolq512_mask ((__v8di)(__m512i)(A), \
@@ -6954,7 +7005,7 @@ _mm512_maskz_ror_epi64 (__mmask8 __U, __m512i __A, int __B)
#define _mm512_ror_epi64(A, B) \
((__m512i)__builtin_ia32_prorq512_mask ((__v8di)(__m512i)(A), \
(int)(B), \
- (__v8di)_mm512_setzero_si512 (), \
+ (__v8di)_mm512_undefined_si512 (), \
(__mmask8)(-1)))
#define _mm512_mask_ror_epi64(W, U, A, B) \
((__m512i)__builtin_ia32_prorq512_mask ((__v8di)(__m512i)(A), \
@@ -6975,7 +7026,7 @@ _mm512_and_si512 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pandd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -6986,7 +7037,7 @@ _mm512_and_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pandd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -7018,7 +7069,7 @@ _mm512_and_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pandq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -7049,7 +7100,7 @@ _mm512_andnot_si512 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pandnd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -7060,7 +7111,7 @@ _mm512_andnot_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pandnd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -7092,7 +7143,7 @@ _mm512_andnot_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pandnq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -7190,7 +7241,7 @@ _mm512_unpackhi_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_punpckhdq512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -7223,7 +7274,7 @@ _mm512_unpackhi_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_punpckhqdq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -7255,7 +7306,7 @@ _mm512_unpacklo_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_punpckldq512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -7288,7 +7339,7 @@ _mm512_unpacklo_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_punpcklqdq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -7571,7 +7622,7 @@ _mm512_movedup_pd (__m512d __A)
{
return (__m512d) __builtin_ia32_movddup512_mask ((__v8df) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -7601,7 +7652,7 @@ _mm512_unpacklo_pd (__m512d __A, __m512d __B)
return (__m512d) __builtin_ia32_unpcklpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -7633,7 +7684,7 @@ _mm512_unpackhi_pd (__m512d __A, __m512d __B)
return (__m512d) __builtin_ia32_unpckhpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1);
}
@@ -7665,7 +7716,7 @@ _mm512_unpackhi_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_unpckhps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -7697,7 +7748,7 @@ _mm512_cvt_roundps_pd (__m256 __A, const int __R)
{
return (__m512d) __builtin_ia32_cvtps2pd512_mask ((__v8sf) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -7727,7 +7778,7 @@ _mm512_cvt_roundph_ps (__m256i __A, const int __R)
{
return (__m512) __builtin_ia32_vcvtph2ps512_mask ((__v16hi) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -7758,7 +7809,7 @@ _mm512_cvt_roundps_ph (__m512 __A, const int __I)
return (__m256i) __builtin_ia32_vcvtps2ph512_mask ((__v16sf) __A,
__I,
(__v16hi)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
-1);
}
@@ -7769,7 +7820,7 @@ _mm512_cvtps_ph (__m512 __A, const int __I)
return (__m256i) __builtin_ia32_vcvtps2ph512_mask ((__v16sf) __A,
__I,
(__v16hi)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
-1);
}
@@ -7817,7 +7868,7 @@ _mm512_maskz_cvtps_ph (__mmask16 __W, __m512 __A, const int __I)
}
#else
#define _mm512_cvt_roundps_pd(A, B) \
- (__m512d)__builtin_ia32_cvtps2pd512_mask(A, (__v8df)_mm512_setzero_pd(), -1, B)
+ (__m512d)__builtin_ia32_cvtps2pd512_mask(A, (__v8df)_mm512_undefined_pd(), -1, B)
#define _mm512_mask_cvt_roundps_pd(W, U, A, B) \
(__m512d)__builtin_ia32_cvtps2pd512_mask(A, (__v8df)(W), U, B)
@@ -7826,7 +7877,7 @@ _mm512_maskz_cvtps_ph (__mmask16 __W, __m512 __A, const int __I)
(__m512d)__builtin_ia32_cvtps2pd512_mask(A, (__v8df)_mm512_setzero_pd(), U, B)
#define _mm512_cvt_roundph_ps(A, B) \
- (__m512)__builtin_ia32_vcvtph2ps512_mask((__v16hi)(A), (__v16sf)_mm512_setzero_ps(), -1, B)
+ (__m512)__builtin_ia32_vcvtph2ps512_mask((__v16hi)(A), (__v16sf)_mm512_undefined_ps(), -1, B)
#define _mm512_mask_cvt_roundph_ps(W, U, A, B) \
(__m512)__builtin_ia32_vcvtph2ps512_mask((__v16hi)(A), (__v16sf)(W), U, B)
@@ -7836,10 +7887,10 @@ _mm512_maskz_cvtps_ph (__mmask16 __W, __m512 __A, const int __I)
#define _mm512_cvt_roundps_ph(A, I) \
((__m256i) __builtin_ia32_vcvtps2ph512_mask ((__v16sf)(__m512) A, (int) (I),\
- (__v16hi)_mm256_setzero_si256 (), -1))
+ (__v16hi)_mm256_undefined_si256 (), -1))
#define _mm512_cvtps_ph(A, I) \
((__m256i) __builtin_ia32_vcvtps2ph512_mask ((__v16sf)(__m512) A, (int) (I),\
- (__v16hi)_mm256_setzero_si256 (), -1))
+ (__v16hi)_mm256_undefined_si256 (), -1))
#define _mm512_mask_cvt_roundps_ph(U, W, A, I) \
((__m256i) __builtin_ia32_vcvtps2ph512_mask ((__v16sf)(__m512) A, (int) (I),\
(__v16hi)(__m256i)(U), (__mmask16) (W)))
@@ -7861,7 +7912,7 @@ _mm512_cvt_roundpd_ps (__m512d __A, const int __R)
{
return (__m256) __builtin_ia32_cvtpd2ps512_mask ((__v8df) __A,
(__v8sf)
- _mm256_setzero_ps (),
+ _mm256_undefined_ps (),
(__mmask8) -1, __R);
}
@@ -7904,7 +7955,7 @@ _mm_cvt_roundss_sd (__m128d __A, __m128 __B, const int __R)
}
#else
#define _mm512_cvt_roundpd_ps(A, B) \
- (__m256)__builtin_ia32_cvtpd2ps512_mask(A, (__v8sf)_mm256_setzero_ps(), -1, B)
+ (__m256)__builtin_ia32_cvtpd2ps512_mask(A, (__v8sf)_mm256_undefined_ps(), -1, B)
#define _mm512_mask_cvt_roundpd_ps(W, U, A, B) \
(__m256)__builtin_ia32_cvtpd2ps512_mask(A, (__v8sf)(W), U, B)
@@ -7972,7 +8023,7 @@ _mm512_getexp_round_ps (__m512 __A, const int __R)
{
return (__m512) __builtin_ia32_getexpps512_mask ((__v16sf) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -8002,7 +8053,7 @@ _mm512_getexp_round_pd (__m512d __A, const int __R)
{
return (__m512d) __builtin_ia32_getexppd512_mask ((__v8df) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -8049,7 +8100,7 @@ _mm512_getmant_round_pd (__m512d __A, _MM_MANTISSA_NORM_ENUM __B,
{
return (__m512d) __builtin_ia32_getmantpd512_mask ((__v8df) __A,
(__C << 2) | __B,
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1, __R);
}
@@ -8085,7 +8136,7 @@ _mm512_getmant_round_ps (__m512 __A, _MM_MANTISSA_NORM_ENUM __B,
{
return (__m512) __builtin_ia32_getmantps512_mask ((__v16sf) __A,
(__C << 2) | __B,
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1, __R);
}
@@ -8142,7 +8193,7 @@ _mm_getmant_round_ss (__m128 __A, __m128 __B,
#define _mm512_getmant_round_pd(X, B, C, R) \
((__m512d)__builtin_ia32_getmantpd512_mask ((__v8df)(__m512d)(X), \
(int)(((C)<<2) | (B)), \
- (__v8df)(__m512d)_mm512_setzero_pd(), \
+ (__v8df)(__m512d)_mm512_undefined_pd(), \
(__mmask8)-1,\
(R)))
@@ -8162,7 +8213,7 @@ _mm_getmant_round_ss (__m128 __A, __m128 __B,
#define _mm512_getmant_round_ps(X, B, C, R) \
((__m512)__builtin_ia32_getmantps512_mask ((__v16sf)(__m512)(X), \
(int)(((C)<<2) | (B)), \
- (__v16sf)(__m512)_mm512_setzero_ps(), \
+ (__v16sf)(__m512)_mm512_undefined_ps(), \
(__mmask16)-1,\
(R)))
@@ -8199,7 +8250,7 @@ _mm_getmant_round_ss (__m128 __A, __m128 __B,
#define _mm512_getexp_round_ps(A, R) \
((__m512)__builtin_ia32_getexpps512_mask((__v16sf)(__m512)(A), \
- (__v16sf)_mm512_setzero_ps(), (__mmask16)-1, R))
+ (__v16sf)_mm512_undefined_ps(), (__mmask16)-1, R))
#define _mm512_mask_getexp_round_ps(W, U, A, R) \
((__m512)__builtin_ia32_getexpps512_mask((__v16sf)(__m512)(A), \
@@ -8211,7 +8262,7 @@ _mm_getmant_round_ss (__m128 __A, __m128 __B,
#define _mm512_getexp_round_pd(A, R) \
((__m512d)__builtin_ia32_getexppd512_mask((__v8df)(__m512d)(A), \
- (__v8df)_mm512_setzero_pd(), (__mmask8)-1, R))
+ (__v8df)_mm512_undefined_pd(), (__mmask8)-1, R))
#define _mm512_mask_getexp_round_pd(W, U, A, R) \
((__m512d)__builtin_ia32_getexppd512_mask((__v8df)(__m512d)(A), \
@@ -8228,7 +8279,9 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_roundscale_round_ps (__m512 __A, const int __imm, const int __R)
{
return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A, __imm,
- (__v16sf) __A, -1, __R);
+ (__v16sf)
+ _mm512_undefined_ps (),
+ -1, __R);
}
extern __inline __m512
@@ -8258,7 +8311,9 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_roundscale_round_pd (__m512d __A, const int __imm, const int __R)
{
return (__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __A, __imm,
- (__v8df) __A, -1, __R);
+ (__v8df)
+ _mm512_undefined_pd (),
+ -1, __R);
}
extern __inline __m512d
@@ -8303,7 +8358,7 @@ _mm_roundscale_round_sd (__m128d __A, __m128d __B, const int __imm,
#else
#define _mm512_roundscale_round_ps(A, B, R) \
((__m512) __builtin_ia32_rndscaleps_mask ((__v16sf)(__m512)(A), (int)(B),\
- (__v16sf)(__m512)(A), (__mmask16)(-1), R))
+ (__v16sf)_mm512_undefined_ps(), (__mmask16)(-1), R))
#define _mm512_mask_roundscale_round_ps(A, B, C, D, R) \
((__m512) __builtin_ia32_rndscaleps_mask ((__v16sf)(__m512)(C), \
(int)(D), \
@@ -8316,7 +8371,7 @@ _mm_roundscale_round_sd (__m128d __A, __m128d __B, const int __imm,
(__mmask16)(A), R))
#define _mm512_roundscale_round_pd(A, B, R) \
((__m512d) __builtin_ia32_rndscalepd_mask ((__v8df)(__m512d)(A), (int)(B),\
- (__v8df)(__m512d)(A), (__mmask8)(-1), R))
+ (__v8df)_mm512_undefined_pd(), (__mmask8)(-1), R))
#define _mm512_mask_roundscale_round_pd(A, B, C, D, R) \
((__m512d) __builtin_ia32_rndscalepd_mask ((__v8df)(__m512d)(C), \
(int)(D), \
@@ -8423,7 +8478,7 @@ _mm512_alignr_epi32 (__m512i __A, __m512i __B, const int __imm)
return (__m512i) __builtin_ia32_alignd512_mask ((__v16si) __A,
(__v16si) __B, __imm,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -8457,7 +8512,7 @@ _mm512_alignr_epi64 (__m512i __A, __m512i __B, const int __imm)
return (__m512i) __builtin_ia32_alignq512_mask ((__v8di) __A,
(__v8di) __B, __imm,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -8486,7 +8541,7 @@ _mm512_maskz_alignr_epi64 (__mmask8 __U, __m512i __A, __m512i __B,
#else
#define _mm512_alignr_epi32(X, Y, C) \
((__m512i)__builtin_ia32_alignd512_mask ((__v16si)(__m512i)(X), \
- (__v16si)(__m512i)(Y), (int)(C), (__v16si)(__m512i)(X), \
+ (__v16si)(__m512i)(Y), (int)(C), (__v16si)_mm512_undefined_si512 (),\
(__mmask16)-1))
#define _mm512_mask_alignr_epi32(W, U, X, Y, C) \
@@ -8496,12 +8551,13 @@ _mm512_maskz_alignr_epi64 (__mmask8 __U, __m512i __A, __m512i __B,
#define _mm512_maskz_alignr_epi32(U, X, Y, C) \
((__m512i)__builtin_ia32_alignd512_mask ((__v16si)(__m512i)(X), \
- (__v16si)(__m512i)(Y), (int)(C), (__v16si)(__m512i)_mm512_setzero_si512 (),\
+ (__v16si)(__m512i)(Y), (int)(C), (__v16si)_mm512_setzero_si512 (),\
(__mmask16)(U)))
#define _mm512_alignr_epi64(X, Y, C) \
((__m512i)__builtin_ia32_alignq512_mask ((__v8di)(__m512i)(X), \
- (__v8di)(__m512i)(Y), (int)(C), (__v8di)(__m512i)(X), (__mmask8)-1))
+ (__v8di)(__m512i)(Y), (int)(C), (__v8di)_mm512_undefined_si512 (), \
+ (__mmask8)-1))
#define _mm512_mask_alignr_epi64(W, U, X, Y, C) \
((__m512i)__builtin_ia32_alignq512_mask ((__v8di)(__m512i)(X), \
@@ -8509,7 +8565,7 @@ _mm512_maskz_alignr_epi64 (__mmask8 __U, __m512i __A, __m512i __B,
#define _mm512_maskz_alignr_epi64(U, X, Y, C) \
((__m512i)__builtin_ia32_alignq512_mask ((__v8di)(__m512i)(X), \
- (__v8di)(__m512i)(Y), (int)(C), (__v8di)(__m512i)_mm512_setzero_si512 (),\
+ (__v8di)(__m512i)(Y), (int)(C), (__v8di)_mm512_setzero_si512 (),\
(__mmask8)(U)))
#endif
@@ -8976,7 +9032,7 @@ extern __inline __m512
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i32gather_ps (__m512i __index, float const *__addr, int __scale)
{
- __m512 v1_old = _mm512_setzero_ps ();
+ __m512 v1_old = _mm512_undefined_ps ();
__mmask16 mask = 0xFFFF;
return (__m512) __builtin_ia32_gathersiv16sf ((__v16sf) v1_old,
@@ -9000,7 +9056,7 @@ extern __inline __m512d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i32gather_pd (__m256i __index, double const *__addr, int __scale)
{
- __m512d v1_old = _mm512_setzero_pd ();
+ __m512d v1_old = _mm512_undefined_pd ();
__mmask8 mask = 0xFF;
return (__m512d) __builtin_ia32_gathersiv8df ((__v8df) v1_old,
@@ -9024,7 +9080,7 @@ extern __inline __m256
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i64gather_ps (__m512i __index, float const *__addr, int __scale)
{
- __m256 v1_old = _mm256_setzero_ps ();
+ __m256 v1_old = _mm256_undefined_ps ();
__mmask8 mask = 0xFF;
return (__m256) __builtin_ia32_gatherdiv16sf ((__v8sf) v1_old,
@@ -9048,7 +9104,7 @@ extern __inline __m512d
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i64gather_pd (__m512i __index, double const *__addr, int __scale)
{
- __m512d v1_old = _mm512_setzero_pd ();
+ __m512d v1_old = _mm512_undefined_pd ();
__mmask8 mask = 0xFF;
return (__m512d) __builtin_ia32_gatherdiv8df ((__v8df) v1_old,
@@ -9072,7 +9128,7 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i32gather_epi32 (__m512i __index, int const *__addr, int __scale)
{
- __m512i v1_old = _mm512_setzero_si512 ();
+ __m512i v1_old = _mm512_undefined_si512 ();
__mmask16 mask = 0xFFFF;
return (__m512i) __builtin_ia32_gathersiv16si ((__v16si) v1_old,
@@ -9096,7 +9152,7 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i32gather_epi64 (__m256i __index, long long const *__addr, int __scale)
{
- __m512i v1_old = _mm512_setzero_si512 ();
+ __m512i v1_old = _mm512_undefined_si512 ();
__mmask8 mask = 0xFF;
return (__m512i) __builtin_ia32_gathersiv8di ((__v8di) v1_old,
@@ -9121,7 +9177,7 @@ extern __inline __m256i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i64gather_epi32 (__m512i __index, int const *__addr, int __scale)
{
- __m256i v1_old = _mm256_setzero_si256 ();
+ __m256i v1_old = _mm256_undefined_si256 ();
__mmask8 mask = 0xFF;
return (__m256i) __builtin_ia32_gatherdiv16si ((__v8si) v1_old,
@@ -9145,7 +9201,7 @@ extern __inline __m512i
__attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_i64gather_epi64 (__m512i __index, long long const *__addr, int __scale)
{
- __m512i v1_old = _mm512_setzero_si512 ();
+ __m512i v1_old = _mm512_undefined_si512 ();
__mmask8 mask = 0xFF;
return (__m512i) __builtin_ia32_gatherdiv8di ((__v8di) v1_old,
@@ -9309,7 +9365,7 @@ _mm512_mask_i64scatter_epi64 (long long *__addr, __mmask8 __mask,
}
#else
#define _mm512_i32gather_ps(INDEX, ADDR, SCALE) \
- (__m512) __builtin_ia32_gathersiv16sf ((__v16sf)_mm512_setzero_ps(), \
+ (__m512) __builtin_ia32_gathersiv16sf ((__v16sf)_mm512_undefined_ps(),\
(float const *)ADDR, \
(__v16si)(__m512i)INDEX, \
(__mmask16)0xFFFF, (int)SCALE)
@@ -9321,7 +9377,7 @@ _mm512_mask_i64scatter_epi64 (long long *__addr, __mmask8 __mask,
(__mmask16)MASK, (int)SCALE)
#define _mm512_i32gather_pd(INDEX, ADDR, SCALE) \
- (__m512d) __builtin_ia32_gathersiv8df ((__v8df)_mm512_setzero_pd(), \
+ (__m512d) __builtin_ia32_gathersiv8df ((__v8df)_mm512_undefined_pd(), \
(double const *)ADDR, \
(__v8si)(__m256i)INDEX, \
(__mmask8)0xFF, (int)SCALE)
@@ -9333,7 +9389,7 @@ _mm512_mask_i64scatter_epi64 (long long *__addr, __mmask8 __mask,
(__mmask8)MASK, (int)SCALE)
#define _mm512_i64gather_ps(INDEX, ADDR, SCALE) \
- (__m256) __builtin_ia32_gatherdiv16sf ((__v8sf)_mm256_setzero_ps(), \
+ (__m256) __builtin_ia32_gatherdiv16sf ((__v8sf)_mm256_undefined_ps(), \
(float const *)ADDR, \
(__v8di)(__m512i)INDEX, \
(__mmask8)0xFF, (int)SCALE)
@@ -9345,7 +9401,7 @@ _mm512_mask_i64scatter_epi64 (long long *__addr, __mmask8 __mask,
(__mmask8)MASK, (int)SCALE)
#define _mm512_i64gather_pd(INDEX, ADDR, SCALE) \
- (__m512d) __builtin_ia32_gatherdiv8df ((__v8df)_mm512_setzero_pd(), \
+ (__m512d) __builtin_ia32_gatherdiv8df ((__v8df)_mm512_undefined_pd(), \
(double const *)ADDR, \
(__v8di)(__m512i)INDEX, \
(__mmask8)0xFF, (int)SCALE)
@@ -9357,7 +9413,7 @@ _mm512_mask_i64scatter_epi64 (long long *__addr, __mmask8 __mask,
(__mmask8)MASK, (int)SCALE)
#define _mm512_i32gather_epi32(INDEX, ADDR, SCALE) \
- (__m512i) __builtin_ia32_gathersiv16si ((__v16si)_mm512_setzero_si512 (), \
+ (__m512i) __builtin_ia32_gathersiv16si ((__v16si)_mm512_undefined_si512 (), \
(int const *)ADDR, \
(__v16si)(__m512i)INDEX, \
(__mmask16)0xFFFF, (int)SCALE)
@@ -9369,7 +9425,7 @@ _mm512_mask_i64scatter_epi64 (long long *__addr, __mmask8 __mask,
(__mmask16)MASK, (int)SCALE)
#define _mm512_i32gather_epi64(INDEX, ADDR, SCALE) \
- (__m512i) __builtin_ia32_gathersiv8di ((__v8di)_mm512_setzero_si512 (), \
+ (__m512i) __builtin_ia32_gathersiv8di ((__v8di)_mm512_undefined_si512 (), \
(long long const *)ADDR, \
(__v8si)(__m256i)INDEX, \
(__mmask8)0xFF, (int)SCALE)
@@ -9381,7 +9437,7 @@ _mm512_mask_i64scatter_epi64 (long long *__addr, __mmask8 __mask,
(__mmask8)MASK, (int)SCALE)
#define _mm512_i64gather_epi32(INDEX, ADDR, SCALE) \
- (__m256i) __builtin_ia32_gatherdiv16si ((__v8si)_mm256_setzero_si256(), \
+ (__m256i) __builtin_ia32_gatherdiv16si ((__v8si)_mm256_undefined_si256(), \
(int const *)ADDR, \
(__v8di)(__m512i)INDEX, \
(__mmask8)0xFF, (int)SCALE)
@@ -9393,7 +9449,7 @@ _mm512_mask_i64scatter_epi64 (long long *__addr, __mmask8 __mask,
(__mmask8)MASK, (int)SCALE)
#define _mm512_i64gather_epi64(INDEX, ADDR, SCALE) \
- (__m512i) __builtin_ia32_gatherdiv8di ((__v8di)_mm512_setzero_si512 (), \
+ (__m512i) __builtin_ia32_gatherdiv8di ((__v8di)_mm512_undefined_si512 (), \
(long long const *)ADDR, \
(__v8di)(__m512i)INDEX, \
(__mmask8)0xFF, (int)SCALE)
@@ -9889,7 +9945,7 @@ _mm512_max_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pmaxsq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -9920,7 +9976,7 @@ _mm512_min_epi64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pminsq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -9951,7 +10007,7 @@ _mm512_max_epu64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pmaxuq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -9982,7 +10038,7 @@ _mm512_min_epu64 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pminuq512_mask ((__v8di) __A,
(__v8di) __B,
(__v8di)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask8) -1);
}
@@ -10013,7 +10069,7 @@ _mm512_max_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pmaxsd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -10044,7 +10100,7 @@ _mm512_min_epi32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pminsd512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -10075,7 +10131,7 @@ _mm512_max_epu32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pmaxud512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -10106,7 +10162,7 @@ _mm512_min_epu32 (__m512i __A, __m512i __B)
return (__m512i) __builtin_ia32_pminud512_mask ((__v16si) __A,
(__v16si) __B,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1);
}
@@ -10137,7 +10193,7 @@ _mm512_unpacklo_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_unpcklps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1);
}
@@ -10382,7 +10438,7 @@ _mm512_sqrt_pd (__m512d __A)
{
return (__m512d) __builtin_ia32_sqrtpd512_mask ((__v8df) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10414,7 +10470,7 @@ _mm512_sqrt_ps (__m512 __A)
{
return (__m512) __builtin_ia32_sqrtps512_mask ((__v16sf) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10447,7 +10503,7 @@ _mm512_add_pd (__m512d __A, __m512d __B)
return (__m512d) __builtin_ia32_addpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10482,7 +10538,7 @@ _mm512_add_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_addps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10517,7 +10573,7 @@ _mm512_sub_pd (__m512d __A, __m512d __B)
return (__m512d) __builtin_ia32_subpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10552,7 +10608,7 @@ _mm512_sub_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_subps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10587,7 +10643,7 @@ _mm512_mul_pd (__m512d __A, __m512d __B)
return (__m512d) __builtin_ia32_mulpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10622,7 +10678,7 @@ _mm512_mul_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_mulps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10657,7 +10713,7 @@ _mm512_div_pd (__m512d __M, __m512d __V)
return (__m512d) __builtin_ia32_divpd512_mask ((__v8df) __M,
(__v8df) __V,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10692,7 +10748,7 @@ _mm512_div_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_divps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10727,7 +10783,7 @@ _mm512_max_pd (__m512d __A, __m512d __B)
return (__m512d) __builtin_ia32_maxpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10762,7 +10818,7 @@ _mm512_max_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_maxps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10797,7 +10853,7 @@ _mm512_min_pd (__m512d __A, __m512d __B)
return (__m512d) __builtin_ia32_minpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10832,7 +10888,7 @@ _mm512_min_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_minps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10867,7 +10923,7 @@ _mm512_scalef_pd (__m512d __A, __m512d __B)
return (__m512d) __builtin_ia32_scalefpd512_mask ((__v8df) __A,
(__v8df) __B,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -10902,7 +10958,7 @@ _mm512_scalef_ps (__m512 __A, __m512 __B)
return (__m512) __builtin_ia32_scalefps512_mask ((__v16sf) __A,
(__v16sf) __B,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11482,7 +11538,7 @@ _mm512_cvttpd_epi32 (__m512d __A)
{
return (__m256i) __builtin_ia32_cvttpd2dq512_mask ((__v8df) __A,
(__v8si)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11514,7 +11570,7 @@ _mm512_cvttpd_epu32 (__m512d __A)
{
return (__m256i) __builtin_ia32_cvttpd2udq512_mask ((__v8df) __A,
(__v8si)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11546,7 +11602,7 @@ _mm512_cvtpd_epi32 (__m512d __A)
{
return (__m256i) __builtin_ia32_cvtpd2dq512_mask ((__v8df) __A,
(__v8si)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11578,7 +11634,7 @@ _mm512_cvtpd_epu32 (__m512d __A)
{
return (__m256i) __builtin_ia32_cvtpd2udq512_mask ((__v8df) __A,
(__v8si)
- _mm256_setzero_si256 (),
+ _mm256_undefined_si256 (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11610,7 +11666,7 @@ _mm512_cvttps_epi32 (__m512 __A)
{
return (__m512i) __builtin_ia32_cvttps2dq512_mask ((__v16sf) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11642,7 +11698,7 @@ _mm512_cvttps_epu32 (__m512 __A)
{
return (__m512i) __builtin_ia32_cvttps2udq512_mask ((__v16sf) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11674,7 +11730,7 @@ _mm512_cvtps_epi32 (__m512 __A)
{
return (__m512i) __builtin_ia32_cvtps2dq512_mask ((__v16sf) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11706,7 +11762,7 @@ _mm512_cvtps_epu32 (__m512 __A)
{
return (__m512i) __builtin_ia32_cvtps2udq512_mask ((__v16sf) __A,
(__v16si)
- _mm512_setzero_si512 (),
+ _mm512_undefined_si512 (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11764,7 +11820,7 @@ _mm512_cvtepi32_ps (__m512i __A)
{
return (__m512) __builtin_ia32_cvtdq2ps512_mask ((__v16si) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -11796,7 +11852,7 @@ _mm512_cvtepu32_ps (__m512i __A)
{
return (__m512) __builtin_ia32_cvtudq2ps512_mask ((__v16si) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12141,7 +12197,7 @@ _mm512_cvtps_pd (__m256 __A)
{
return (__m512d) __builtin_ia32_cvtps2pd512_mask ((__v8sf) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12173,7 +12229,7 @@ _mm512_cvtph_ps (__m256i __A)
{
return (__m512) __builtin_ia32_vcvtph2ps512_mask ((__v16hi) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12205,7 +12261,7 @@ _mm512_cvtpd_ps (__m512d __A)
{
return (__m256) __builtin_ia32_cvtpd2ps512_mask ((__v8df) __A,
(__v8sf)
- _mm256_setzero_ps (),
+ _mm256_undefined_ps (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12238,7 +12294,7 @@ _mm512_getexp_ps (__m512 __A)
{
return (__m512) __builtin_ia32_getexpps512_mask ((__v16sf) __A,
(__v16sf)
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12270,7 +12326,7 @@ _mm512_getexp_pd (__m512d __A)
{
return (__m512d) __builtin_ia32_getexppd512_mask ((__v8df) __A,
(__v8df)
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12321,7 +12377,7 @@ _mm512_getmant_pd (__m512d __A, _MM_MANTISSA_NORM_ENUM __B,
{
return (__m512d) __builtin_ia32_getmantpd512_mask ((__v8df) __A,
(__C << 2) | __B,
- _mm512_setzero_pd (),
+ _mm512_undefined_pd (),
(__mmask8) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12357,7 +12413,7 @@ _mm512_getmant_ps (__m512 __A, _MM_MANTISSA_NORM_ENUM __B,
{
return (__m512) __builtin_ia32_getmantps512_mask ((__v16sf) __A,
(__C << 2) | __B,
- _mm512_setzero_ps (),
+ _mm512_undefined_ps (),
(__mmask16) -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12412,7 +12468,7 @@ _mm_getmant_ss (__m128 __A, __m128 __B, _MM_MANTISSA_NORM_ENUM __C,
#define _mm512_getmant_pd(X, B, C) \
((__m512d)__builtin_ia32_getmantpd512_mask ((__v8df)(__m512d)(X), \
(int)(((C)<<2) | (B)), \
- (__v8df)(__m512d)_mm512_setzero_pd(), \
+ (__v8df)_mm512_undefined_pd(), \
(__mmask8)-1,\
_MM_FROUND_CUR_DIRECTION))
@@ -12426,13 +12482,13 @@ _mm_getmant_ss (__m128 __A, __m128 __B, _MM_MANTISSA_NORM_ENUM __C,
#define _mm512_maskz_getmant_pd(U, X, B, C) \
((__m512d)__builtin_ia32_getmantpd512_mask ((__v8df)(__m512d)(X), \
(int)(((C)<<2) | (B)), \
- (__v8df)(__m512d)_mm512_setzero_pd(), \
+ (__v8df)_mm512_setzero_pd(), \
(__mmask8)(U),\
_MM_FROUND_CUR_DIRECTION))
#define _mm512_getmant_ps(X, B, C) \
((__m512)__builtin_ia32_getmantps512_mask ((__v16sf)(__m512)(X), \
(int)(((C)<<2) | (B)), \
- (__v16sf)(__m512)_mm512_setzero_ps(), \
+ (__v16sf)_mm512_undefined_ps(), \
(__mmask16)-1,\
_MM_FROUND_CUR_DIRECTION))
@@ -12446,7 +12502,7 @@ _mm_getmant_ss (__m128 __A, __m128 __B, _MM_MANTISSA_NORM_ENUM __C,
#define _mm512_maskz_getmant_ps(U, X, B, C) \
((__m512)__builtin_ia32_getmantps512_mask ((__v16sf)(__m512)(X), \
(int)(((C)<<2) | (B)), \
- (__v16sf)(__m512)_mm512_setzero_ps(), \
+ (__v16sf)_mm512_setzero_ps(), \
(__mmask16)(U),\
_MM_FROUND_CUR_DIRECTION))
#define _mm_getmant_sd(X, Y, C, D) \
@@ -12471,7 +12527,7 @@ _mm_getmant_ss (__m128 __A, __m128 __B, _MM_MANTISSA_NORM_ENUM __C,
#define _mm512_getexp_ps(A) \
((__m512)__builtin_ia32_getexpps512_mask((__v16sf)(__m512)(A), \
- (__v16sf)_mm512_setzero_ps(), (__mmask16)-1, _MM_FROUND_CUR_DIRECTION))
+ (__v16sf)_mm512_undefined_ps(), (__mmask16)-1, _MM_FROUND_CUR_DIRECTION))
#define _mm512_mask_getexp_ps(W, U, A) \
((__m512)__builtin_ia32_getexpps512_mask((__v16sf)(__m512)(A), \
@@ -12483,7 +12539,7 @@ _mm_getmant_ss (__m128 __A, __m128 __B, _MM_MANTISSA_NORM_ENUM __C,
#define _mm512_getexp_pd(A) \
((__m512d)__builtin_ia32_getexppd512_mask((__v8df)(__m512d)(A), \
- (__v8df)_mm512_setzero_pd(), (__mmask8)-1, _MM_FROUND_CUR_DIRECTION))
+ (__v8df)_mm512_undefined_pd(), (__mmask8)-1, _MM_FROUND_CUR_DIRECTION))
#define _mm512_mask_getexp_pd(W, U, A) \
((__m512d)__builtin_ia32_getexppd512_mask((__v8df)(__m512d)(A), \
@@ -12500,7 +12556,9 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_roundscale_ps (__m512 __A, const int __imm)
{
return (__m512) __builtin_ia32_rndscaleps_mask ((__v16sf) __A, __imm,
- (__v16sf) __A, -1,
+ (__v16sf)
+ _mm512_undefined_ps (),
+ -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12532,7 +12590,9 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__))
_mm512_roundscale_pd (__m512d __A, const int __imm)
{
return (__m512d) __builtin_ia32_rndscalepd_mask ((__v8df) __A, __imm,
- (__v8df) __A, -1,
+ (__v8df)
+ _mm512_undefined_pd (),
+ -1,
_MM_FROUND_CUR_DIRECTION);
}
@@ -12580,7 +12640,7 @@ _mm_roundscale_sd (__m128d __A, __m128d __B, const int __imm)
#else
#define _mm512_roundscale_ps(A, B) \
((__m512) __builtin_ia32_rndscaleps_mask ((__v16sf)(__m512)(A), (int)(B),\
- (__v16sf)(__m512)(A), (__mmask16)(-1), _MM_FROUND_CUR_DIRECTION))
+ (__v16sf)_mm512_undefined_ps(), (__mmask16)(-1), _MM_FROUND_CUR_DIRECTION))
#define _mm512_mask_roundscale_ps(A, B, C, D) \
((__m512) __builtin_ia32_rndscaleps_mask ((__v16sf)(__m512)(C), \
(int)(D), \
@@ -12593,7 +12653,7 @@ _mm_roundscale_sd (__m128d __A, __m128d __B, const int __imm)
(__mmask16)(A), _MM_FROUND_CUR_DIRECTION))
#define _mm512_roundscale_pd(A, B) \
((__m512d) __builtin_ia32_rndscalepd_mask ((__v8df)(__m512d)(A), (int)(B),\
- (__v8df)(__m512d)(A), (__mmask8)(-1), _MM_FROUND_CUR_DIRECTION))
+ (__v8df)_mm512_undefined_pd(), (__mmask8)(-1), _MM_FROUND_CUR_DIRECTION))
#define _mm512_mask_roundscale_pd(A, B, C, D) \
((__m512d) __builtin_ia32_rndscalepd_mask ((__v8df)(__m512d)(C), \
(int)(D), \
diff --git a/gcc/config/i386/avxintrin.h b/gcc/config/i386/avxintrin.h
index f960b76..2ea327c 100644
--- a/gcc/config/i386/avxintrin.h
+++ b/gcc/config/i386/avxintrin.h
@@ -1168,6 +1168,27 @@ _mm256_movemask_ps (__m256 __A)
}
extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm256_undefined_pd (void)
+{
+ __m256d __Y = __Y;
+ return __Y;
+}
+
+extern __inline __m256 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm256_undefined_ps (void)
+{
+ __m256 __Y = __Y;
+ return __Y;
+}
+
+extern __inline __m256i __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm256_undefined_si256 (void)
+{
+ __m256i __Y = __Y;
+ return __Y;
+}
+
+extern __inline __m256d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm256_setzero_pd (void)
{
return __extension__ (__m256d){ 0.0, 0.0, 0.0, 0.0 };
diff --git a/gcc/config/i386/emmintrin.h b/gcc/config/i386/emmintrin.h
index 08928fb..a2bdf0e 100644
--- a/gcc/config/i386/emmintrin.h
+++ b/gcc/config/i386/emmintrin.h
@@ -86,6 +86,14 @@ _mm_setr_pd (double __W, double __X)
return __extension__ (__m128d){ __W, __X };
}
+/* Create an undefined vector. */
+extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm_undefined_pd (void)
+{
+ __m128d __Y = __Y;
+ return __Y;
+}
+
/* Create a vector of zeros. */
extern __inline __m128d __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm_setzero_pd (void)
@@ -728,6 +736,14 @@ _mm_move_epi64 (__m128i __A)
return (__m128i)__builtin_ia32_movq128 ((__v2di) __A);
}
+/* Create an undefined vector. */
+extern __inline __m128i __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm_undefined_si128 (void)
+{
+ __m128i __Y = __Y;
+ return __Y;
+}
+
/* Create a vector of zeros. */
extern __inline __m128i __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm_setzero_si128 (void)
diff --git a/gcc/config/i386/xmmintrin.h b/gcc/config/i386/xmmintrin.h
index 0238439..a3824e7 100644
--- a/gcc/config/i386/xmmintrin.h
+++ b/gcc/config/i386/xmmintrin.h
@@ -102,6 +102,14 @@ typedef float __v4sf __attribute__ ((__vector_size__ (16)));
#define _MM_FLUSH_ZERO_ON 0x8000
#define _MM_FLUSH_ZERO_OFF 0x0000
+/* Create an undefined vector. */
+extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
+_mm_undefined_ps (void)
+{
+ __m128 __Y = __Y;
+ return __Y;
+}
+
/* Create a vector of zeros. */
extern __inline __m128 __attribute__((__gnu_inline__, __always_inline__, __artificial__))
_mm_setzero_ps (void)
More information about the Gcc-patches
mailing list