diff --git a/gcc/ChangeLog b/gcc/ChangeLog index a360693d1d8b..e6ba30f614c8 100644 --- a/gcc/ChangeLog +++ b/gcc/ChangeLog @@ -1,3 +1,30 @@ +2016-08-22 Uros Bizjak + + Backport from mainline + 2016-08-14 Uros Bizjak + + PR target/76342 + * config/i386/avx512fintrin.h (_mm512_undefined_epi32): + Renamed from _mm512_undefined_si512. + (_mm_undefined_si512): New definition. + + Backport from mainline: + 2016-08-09 David Wohlferd + + * config/i3836/avx512fintrin.h (_mm512_cvtsepi64_epi32): Remove + unused variable __O. + + Backport from mainline: + 2016-08-09 Uros Bizjak + + PR target/72843 + * config/i386/i386.md (*movtf_internal): Use + lra_in_progress || reload_completed instead of !can_create_pseudo_p + in the insn constraint. + (*movxf_internal): Ditto. + (*movdf_internal): Ditto. + (*movsf_internal): Ditto. + 2016-08-18 Oleg Endo Backport from mainline diff --git a/gcc/config/i386/avx512bwintrin.h b/gcc/config/i386/avx512bwintrin.h index 3114849fdd14..7a7ed68c997c 100644 --- a/gcc/config/i386/avx512bwintrin.h +++ b/gcc/config/i386/avx512bwintrin.h @@ -270,9 +270,8 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) _mm512_broadcastb_epi8 (__m128i __A) { return (__m512i) __builtin_ia32_pbroadcastb512_mask ((__v16qi) __A, - (__v64qi)_mm512_undefined_si512(), - (__mmask64) - - 1); + (__v64qi)_mm512_undefined_epi32(), + (__mmask64) -1); } extern __inline __m512i @@ -318,8 +317,8 @@ __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) _mm512_broadcastw_epi16 (__m128i __A) { return (__m512i) __builtin_ia32_pbroadcastw512_mask ((__v8hi) __A, - (__v32hi)_mm512_undefined_si512(), - (__mmask32)-1); + (__v32hi)_mm512_undefined_epi32(), + (__mmask32) -1); } extern __inline __m512i @@ -588,8 +587,7 @@ _mm512_permutex2var_epi16 (__m512i __A, __m512i __I, __m512i __B) /* idx */ , (__v32hi) __A, (__v32hi) __B, - (__mmask32) - - 1); + (__mmask32) -1); } extern __inline __m512i @@ -2284,7 +2282,7 @@ _mm512_cmpneq_epu8_mask (__m512i __X, __m512i __Y) { return (__mmask64) __builtin_ia32_ucmpb512_mask ((__v64qi) __X, (__v64qi) __Y, 4, - (__mmask64) - 1); + (__mmask64) -1); } extern __inline __mmask64 @@ -2293,7 +2291,7 @@ _mm512_cmplt_epu8_mask (__m512i __X, __m512i __Y) { return (__mmask64) __builtin_ia32_ucmpb512_mask ((__v64qi) __X, (__v64qi) __Y, 1, - (__mmask64) - 1); + (__mmask64) -1); } extern __inline __mmask64 @@ -2302,7 +2300,7 @@ _mm512_cmpge_epu8_mask (__m512i __X, __m512i __Y) { return (__mmask64) __builtin_ia32_ucmpb512_mask ((__v64qi) __X, (__v64qi) __Y, 5, - (__mmask64) - 1); + (__mmask64) -1); } extern __inline __mmask64 @@ -2311,7 +2309,7 @@ _mm512_cmple_epu8_mask (__m512i __X, __m512i __Y) { return (__mmask64) __builtin_ia32_ucmpb512_mask ((__v64qi) __X, (__v64qi) __Y, 2, - (__mmask64) - 1); + (__mmask64) -1); } extern __inline __mmask32 @@ -2320,7 +2318,7 @@ _mm512_cmpneq_epu16_mask (__m512i __X, __m512i __Y) { return (__mmask32) __builtin_ia32_ucmpw512_mask ((__v32hi) __X, (__v32hi) __Y, 4, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2329,7 +2327,7 @@ _mm512_cmplt_epu16_mask (__m512i __X, __m512i __Y) { return (__mmask32) __builtin_ia32_ucmpw512_mask ((__v32hi) __X, (__v32hi) __Y, 1, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2338,7 +2336,7 @@ _mm512_cmpge_epu16_mask (__m512i __X, __m512i __Y) { return (__mmask32) __builtin_ia32_ucmpw512_mask ((__v32hi) __X, (__v32hi) __Y, 5, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2347,7 +2345,7 @@ _mm512_cmple_epu16_mask (__m512i __X, __m512i __Y) { return (__mmask32) __builtin_ia32_ucmpw512_mask ((__v32hi) __X, (__v32hi) __Y, 2, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask64 @@ -2356,7 +2354,7 @@ _mm512_cmpneq_epi8_mask (__m512i __X, __m512i __Y) { return (__mmask64) __builtin_ia32_cmpb512_mask ((__v64qi) __X, (__v64qi) __Y, 4, - (__mmask64) - 1); + (__mmask64) -1); } extern __inline __mmask64 @@ -2365,7 +2363,7 @@ _mm512_cmplt_epi8_mask (__m512i __X, __m512i __Y) { return (__mmask64) __builtin_ia32_cmpb512_mask ((__v64qi) __X, (__v64qi) __Y, 1, - (__mmask64) - 1); + (__mmask64) -1); } extern __inline __mmask64 @@ -2374,7 +2372,7 @@ _mm512_cmpge_epi8_mask (__m512i __X, __m512i __Y) { return (__mmask64) __builtin_ia32_cmpb512_mask ((__v64qi) __X, (__v64qi) __Y, 5, - (__mmask64) - 1); + (__mmask64) -1); } extern __inline __mmask64 @@ -2383,7 +2381,7 @@ _mm512_cmple_epi8_mask (__m512i __X, __m512i __Y) { return (__mmask64) __builtin_ia32_cmpb512_mask ((__v64qi) __X, (__v64qi) __Y, 2, - (__mmask64) - 1); + (__mmask64) -1); } extern __inline __mmask32 @@ -2392,7 +2390,7 @@ _mm512_cmpneq_epi16_mask (__m512i __X, __m512i __Y) { return (__mmask32) __builtin_ia32_cmpw512_mask ((__v32hi) __X, (__v32hi) __Y, 4, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2401,7 +2399,7 @@ _mm512_cmplt_epi16_mask (__m512i __X, __m512i __Y) { return (__mmask32) __builtin_ia32_cmpw512_mask ((__v32hi) __X, (__v32hi) __Y, 1, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2410,7 +2408,7 @@ _mm512_cmpge_epi16_mask (__m512i __X, __m512i __Y) { return (__mmask32) __builtin_ia32_cmpw512_mask ((__v32hi) __X, (__v32hi) __Y, 5, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2419,7 +2417,7 @@ _mm512_cmple_epi16_mask (__m512i __X, __m512i __Y) { return (__mmask32) __builtin_ia32_cmpw512_mask ((__v32hi) __X, (__v32hi) __Y, 2, - (__mmask32) - 1); + (__mmask32) -1); } #ifdef __OPTIMIZE__ diff --git a/gcc/config/i386/avx512dqintrin.h b/gcc/config/i386/avx512dqintrin.h index b36ef48f2a17..dd46f72a8eef 100644 --- a/gcc/config/i386/avx512dqintrin.h +++ b/gcc/config/i386/avx512dqintrin.h @@ -41,8 +41,7 @@ _mm512_broadcast_f64x2 (__m128d __A) return (__m512d) __builtin_ia32_broadcastf64x2_512_mask ((__v2df) __A, _mm512_undefined_pd(), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m512d @@ -72,9 +71,8 @@ _mm512_broadcast_i64x2 (__m128i __A) { return (__m512i) __builtin_ia32_broadcasti64x2_512_mask ((__v2di) __A, - _mm512_undefined_si512(), - (__mmask8) - - 1); + _mm512_undefined_epi32(), + (__mmask8) -1); } extern __inline __m512i @@ -104,8 +102,7 @@ _mm512_broadcast_f32x2 (__m128 __A) { return (__m512) __builtin_ia32_broadcastf32x2_512_mask ((__v4sf) __A, (__v16sf)_mm512_undefined_ps(), - (__mmask16) - - 1); + (__mmask16) -1); } extern __inline __m512 @@ -133,9 +130,8 @@ _mm512_broadcast_i32x2 (__m128i __A) { return (__m512i) __builtin_ia32_broadcasti32x2_512_mask ((__v4si) __A, - (__v16si)_mm512_undefined_si512(), - (__mmask16) - -1); + (__v16si)_mm512_undefined_epi32(), + (__mmask16) -1); } extern __inline __m512i @@ -165,8 +161,7 @@ _mm512_broadcast_f32x8 (__m256 __A) { return (__m512) __builtin_ia32_broadcastf32x8_512_mask ((__v8sf) __A, _mm512_undefined_ps(), - (__mmask16) - - 1); + (__mmask16) -1); } extern __inline __m512 @@ -194,9 +189,8 @@ _mm512_broadcast_i32x8 (__m256i __A) { return (__m512i) __builtin_ia32_broadcasti32x8_512_mask ((__v8si) __A, - (__v16si)_mm512_undefined_si512(), - (__mmask16) - -1); + (__v16si)_mm512_undefined_epi32(), + (__mmask16) -1); } extern __inline __m512i @@ -1569,8 +1563,7 @@ _mm512_extractf64x2_pd (__m512d __A, const int __imm) __imm, (__v2df) _mm_setzero_pd (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128d @@ -1640,8 +1633,7 @@ _mm512_extracti64x2_epi64 (__m512i __A, const int __imm) __imm, (__v2di) _mm_setzero_di (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128i @@ -1829,8 +1821,7 @@ _mm512_inserti64x2 (__m512i __A, __m128i __B, const int __imm) __imm, (__v8di) _mm512_setzero_si512 (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m512i @@ -1869,8 +1860,7 @@ _mm512_insertf64x2 (__m512d __A, __m128d __B, const int __imm) __imm, (__v8df) _mm512_setzero_pd (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m512d @@ -1933,8 +1923,7 @@ _mm512_fpclass_ps_mask (__m512 __A, const int __imm) { return (__mmask16) __builtin_ia32_fpclassps512_mask ((__v16sf) __A, __imm, - (__mmask16) - - 1); + (__mmask16) -1); } #else diff --git a/gcc/config/i386/avx512fintrin.h b/gcc/config/i386/avx512fintrin.h index 5d71bd6c5b66..184e9e88d648 100644 --- a/gcc/config/i386/avx512fintrin.h +++ b/gcc/config/i386/avx512fintrin.h @@ -130,12 +130,14 @@ _mm512_undefined_pd (void) extern __inline __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_undefined_si512 (void) +_mm512_undefined_epi32 (void) { __m512i __Y = __Y; return __Y; } +#define _mm512_undefined_si512 _mm512_undefined_epi32 + extern __inline __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) _mm512_set1_epi8 (char __A) @@ -549,7 +551,7 @@ _mm512_sllv_epi32 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_psllv16si_mask ((__v16si) __X, (__v16si) __Y, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -581,7 +583,7 @@ _mm512_srav_epi32 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_psrav16si_mask ((__v16si) __X, (__v16si) __Y, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -613,7 +615,7 @@ _mm512_srlv_epi32 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_psrlv16si_mask ((__v16si) __X, (__v16si) __Y, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -733,7 +735,7 @@ _mm512_srav_epi64 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_psrav8di_mask ((__v8di) __X, (__v8di) __Y, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -765,7 +767,7 @@ _mm512_srlv_epi64 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_psrlv8di_mask ((__v8di) __X, (__v8di) __Y, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -825,7 +827,7 @@ _mm512_mul_epi32 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_pmuldq512_mask ((__v16si) __X, (__v16si) __Y, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -884,7 +886,7 @@ _mm512_mul_epu32 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_pmuludq512_mask ((__v16si) __X, (__v16si) __Y, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -915,7 +917,7 @@ _mm512_slli_epi64 (__m512i __A, unsigned int __B) { return (__m512i) __builtin_ia32_psllqi512_mask ((__v8di) __A, __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -941,7 +943,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_undefined_si512 (),\ + (__v8di)(__m512i)_mm512_undefined_epi32 (),\ (__mmask8)-1)) #define _mm512_mask_slli_epi64(W, U, X, C) \ @@ -962,7 +964,7 @@ _mm512_sll_epi64 (__m512i __A, __m128i __B) return (__m512i) __builtin_ia32_psllq512_mask ((__v8di) __A, (__v2di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -994,7 +996,7 @@ _mm512_srli_epi64 (__m512i __A, unsigned int __B) { return (__m512i) __builtin_ia32_psrlqi512_mask ((__v8di) __A, __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -1020,7 +1022,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_undefined_si512 (),\ + (__v8di)(__m512i)_mm512_undefined_epi32 (),\ (__mmask8)-1)) #define _mm512_mask_srli_epi64(W, U, X, C) \ @@ -1041,7 +1043,7 @@ _mm512_srl_epi64 (__m512i __A, __m128i __B) return (__m512i) __builtin_ia32_psrlq512_mask ((__v8di) __A, (__v2di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -1073,7 +1075,7 @@ _mm512_srai_epi64 (__m512i __A, unsigned int __B) { return (__m512i) __builtin_ia32_psraqi512_mask ((__v8di) __A, __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -1099,7 +1101,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_undefined_si512 (),\ + (__v8di)(__m512i)_mm512_undefined_epi32 (),\ (__mmask8)-1)) #define _mm512_mask_srai_epi64(W, U, X, C) \ @@ -1120,7 +1122,7 @@ _mm512_sra_epi64 (__m512i __A, __m128i __B) return (__m512i) __builtin_ia32_psraq512_mask ((__v8di) __A, (__v2di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -1152,7 +1154,7 @@ _mm512_slli_epi32 (__m512i __A, unsigned int __B) { return (__m512i) __builtin_ia32_pslldi512_mask ((__v16si) __A, __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1178,7 +1180,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_undefined_si512 (),\ + (__v16si)(__m512i)_mm512_undefined_epi32 (),\ (__mmask16)-1)) #define _mm512_mask_slli_epi32(W, U, X, C) \ @@ -1199,7 +1201,7 @@ _mm512_sll_epi32 (__m512i __A, __m128i __B) return (__m512i) __builtin_ia32_pslld512_mask ((__v16si) __A, (__v4si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1231,7 +1233,7 @@ _mm512_srli_epi32 (__m512i __A, unsigned int __B) { return (__m512i) __builtin_ia32_psrldi512_mask ((__v16si) __A, __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1257,7 +1259,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_undefined_si512 (),\ + (__v16si)(__m512i)_mm512_undefined_epi32 (),\ (__mmask16)-1)) #define _mm512_mask_srli_epi32(W, U, X, C) \ @@ -1278,7 +1280,7 @@ _mm512_srl_epi32 (__m512i __A, __m128i __B) return (__m512i) __builtin_ia32_psrld512_mask ((__v16si) __A, (__v4si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1310,7 +1312,7 @@ _mm512_srai_epi32 (__m512i __A, unsigned int __B) { return (__m512i) __builtin_ia32_psradi512_mask ((__v16si) __A, __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1336,7 +1338,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_undefined_si512 (),\ + (__v16si)(__m512i)_mm512_undefined_epi32 (),\ (__mmask16)-1)) #define _mm512_mask_srai_epi32(W, U, X, C) \ @@ -1357,7 +1359,7 @@ _mm512_sra_epi32 (__m512i __A, __m128i __B) return (__m512i) __builtin_ia32_psrad512_mask ((__v16si) __A, (__v4si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1778,7 +1780,7 @@ _mm512_cvtepi8_epi32 (__m128i __A) { return (__m512i) __builtin_ia32_pmovsxbd512_mask ((__v16qi) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1807,7 +1809,7 @@ _mm512_cvtepi8_epi64 (__m128i __A) { return (__m512i) __builtin_ia32_pmovsxbq512_mask ((__v16qi) __A, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -1836,7 +1838,7 @@ _mm512_cvtepi16_epi32 (__m256i __A) { return (__m512i) __builtin_ia32_pmovsxwd512_mask ((__v16hi) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1865,7 +1867,7 @@ _mm512_cvtepi16_epi64 (__m128i __A) { return (__m512i) __builtin_ia32_pmovsxwq512_mask ((__v8hi) __A, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -1894,7 +1896,7 @@ _mm512_cvtepi32_epi64 (__m256i __X) { return (__m512i) __builtin_ia32_pmovsxdq512_mask ((__v8si) __X, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -1923,7 +1925,7 @@ _mm512_cvtepu8_epi32 (__m128i __A) { return (__m512i) __builtin_ia32_pmovzxbd512_mask ((__v16qi) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -1952,7 +1954,7 @@ _mm512_cvtepu8_epi64 (__m128i __A) { return (__m512i) __builtin_ia32_pmovzxbq512_mask ((__v16qi) __A, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -1981,7 +1983,7 @@ _mm512_cvtepu16_epi32 (__m256i __A) { return (__m512i) __builtin_ia32_pmovzxwd512_mask ((__v16hi) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -2010,7 +2012,7 @@ _mm512_cvtepu16_epi64 (__m128i __A) { return (__m512i) __builtin_ia32_pmovzxwq512_mask ((__v8hi) __A, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -2039,7 +2041,7 @@ _mm512_cvtepu32_epi64 (__m256i __X) { return (__m512i) __builtin_ia32_pmovzxdq512_mask ((__v8si) __X, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -3407,7 +3409,7 @@ _mm512_abs_epi64 (__m512i __A) { return (__m512i) __builtin_ia32_pabsq512_mask ((__v8di) __A, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -3436,7 +3438,7 @@ _mm512_abs_epi32 (__m512i __A) { return (__m512i) __builtin_ia32_pabsd512_mask ((__v16si) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -3521,7 +3523,7 @@ _mm512_broadcastd_epi32 (__m128i __A) { return (__m512i) __builtin_ia32_pbroadcastd512 ((__v4si) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -3549,7 +3551,7 @@ _mm512_set1_epi32 (int __A) { return (__m512i) __builtin_ia32_pbroadcastd512_gpr_mask (__A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16)(-1)); } @@ -3577,7 +3579,7 @@ _mm512_broadcastq_epi64 (__m128i __A) { return (__m512i) __builtin_ia32_pbroadcastq512 ((__v2di) __A, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -3605,7 +3607,7 @@ _mm512_set1_epi64 (long long __A) { return (__m512i) __builtin_ia32_pbroadcastq512_gpr_mask (__A, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8)(-1)); } @@ -3662,7 +3664,7 @@ _mm512_broadcast_i32x4 (__m128i __A) { return (__m512i) __builtin_ia32_broadcasti32x4_512 ((__v4si) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -3720,7 +3722,7 @@ _mm512_broadcast_i64x4 (__m256i __A) { return (__m512i) __builtin_ia32_broadcasti64x4_512 ((__v4di) __A, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -3841,7 +3843,7 @@ _mm512_shuffle_epi32 (__m512i __A, _MM_PERM_ENUM __mask) return (__m512i) __builtin_ia32_pshufd512_mask ((__v16si) __A, __mask, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -3874,7 +3876,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_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -3909,7 +3911,7 @@ _mm512_shuffle_i32x4 (__m512i __A, __m512i __B, const int __imm) (__v16si) __B, __imm, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -4009,7 +4011,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_undefined_si512 (),\ + (__v16si)(__m512i)_mm512_undefined_epi32 (),\ (__mmask16)-1)) #define _mm512_mask_shuffle_epi32(W, U, X, C) \ @@ -4025,7 +4027,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_undefined_si512 (),\ + (__v8di)(__m512i)_mm512_undefined_epi32 (),\ (__mmask8)-1)) #define _mm512_mask_shuffle_i64x2(W, U, X, Y, C) \ @@ -4043,7 +4045,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_undefined_si512 (),\ + (__v16si)(__m512i)_mm512_undefined_epi32 (),\ (__mmask16)-1)) #define _mm512_mask_shuffle_i32x4(W, U, X, Y, C) \ @@ -4102,7 +4104,7 @@ _mm512_rolv_epi32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_prolvd512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -4134,7 +4136,7 @@ _mm512_rorv_epi32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_prorvd512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -4166,7 +4168,7 @@ _mm512_rolv_epi64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_prolvq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -4198,7 +4200,7 @@ _mm512_rorv_epi64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_prorvq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -4390,7 +4392,7 @@ _mm512_cvtt_roundps_epi32 (__m512 __A, const int __R) { return (__m512i) __builtin_ia32_cvttps2dq512_mask ((__v16sf) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1, __R); } @@ -4420,7 +4422,7 @@ _mm512_cvtt_roundps_epu32 (__m512 __A, const int __R) { return (__m512i) __builtin_ia32_cvttps2udq512_mask ((__v16sf) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1, __R); } @@ -4445,7 +4447,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_undefined_si512 (), -1, B)) + ((__m512i)__builtin_ia32_cvttps2dq512_mask(A, (__v16si)_mm512_undefined_epi32 (), -1, B)) #define _mm512_mask_cvtt_roundps_epi32(W, U, A, B) \ ((__m512i)__builtin_ia32_cvttps2dq512_mask(A, (__v16si)(W), U, B)) @@ -4454,7 +4456,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_undefined_si512 (), -1, B)) + ((__m512i)__builtin_ia32_cvttps2udq512_mask(A, (__v16si)_mm512_undefined_epi32 (), -1, B)) #define _mm512_mask_cvtt_roundps_epu32(W, U, A, B) \ ((__m512i)__builtin_ia32_cvttps2udq512_mask(A, (__v16si)(W), U, B)) @@ -4470,7 +4472,7 @@ _mm512_cvt_roundps_epi32 (__m512 __A, const int __R) { return (__m512i) __builtin_ia32_cvtps2dq512_mask ((__v16sf) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1, __R); } @@ -4500,7 +4502,7 @@ _mm512_cvt_roundps_epu32 (__m512 __A, const int __R) { return (__m512i) __builtin_ia32_cvtps2udq512_mask ((__v16sf) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1, __R); } @@ -4525,7 +4527,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_undefined_si512 (), -1, B)) + ((__m512i)__builtin_ia32_cvtps2dq512_mask(A, (__v16si)_mm512_undefined_epi32 (), -1, B)) #define _mm512_mask_cvt_roundps_epi32(W, U, A, B) \ ((__m512i)__builtin_ia32_cvtps2dq512_mask(A, (__v16si)(W), U, B)) @@ -4534,7 +4536,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_undefined_si512 (), -1, B)) + ((__m512i)__builtin_ia32_cvtps2udq512_mask(A, (__v16si)_mm512_undefined_epi32 (), -1, B)) #define _mm512_mask_cvt_roundps_epu32(W, U, A, B) \ ((__m512i)__builtin_ia32_cvtps2udq512_mask(A, (__v16si)(W), U, B)) @@ -4903,7 +4905,6 @@ extern __inline __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) _mm512_cvtsepi64_epi32 (__m512i __A) { - __v8si __O; return (__m256i) __builtin_ia32_pmovsqd512_mask ((__v8di) __A, (__v8si) _mm256_undefined_si256 (), @@ -5556,7 +5557,7 @@ _mm512_inserti64x4 (__m512i __A, __m256i __B, const int __imm) (__v4di) __B, __imm, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -5651,7 +5652,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_undefined_si512 (), \ + (__v8di)(__m512i)_mm512_undefined_epi32 (), \ (__mmask8)-1)) #define _mm512_mask_inserti64x4(W, U, X, Y, C) \ @@ -6177,7 +6178,7 @@ _mm512_permutex_epi64 (__m512i __X, const int __I) { return (__m512i) __builtin_ia32_permdi512_mask ((__v8di) __X, __I, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) (-1)); } @@ -6248,7 +6249,7 @@ _mm512_maskz_permutex_pd (__mmask8 __U, __m512d __X, const int __M) ((__m512i) __builtin_ia32_permdi512_mask ((__v8di)(__m512i)(X), \ (int)(I), \ (__v8di)(__m512i) \ - (_mm512_undefined_si512 ()),\ + (_mm512_undefined_epi32 ()),\ (__mmask8)(-1))) #define _mm512_maskz_permutex_epi64(M, X, I) \ @@ -6283,7 +6284,7 @@ _mm512_permutexvar_epi64 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_permvardi512_mask ((__v8di) __Y, (__v8di) __X, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -6316,7 +6317,7 @@ _mm512_permutexvar_epi32 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_permvarsi512_mask ((__v16si) __Y, (__v16si) __X, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -6891,7 +6892,7 @@ _mm512_rol_epi32 (__m512i __A, const int __B) { return (__m512i) __builtin_ia32_prold512_mask ((__v16si) __A, __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -6920,7 +6921,7 @@ _mm512_ror_epi32 (__m512i __A, int __B) { return (__m512i) __builtin_ia32_prord512_mask ((__v16si) __A, __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -6949,7 +6950,7 @@ _mm512_rol_epi64 (__m512i __A, const int __B) { return (__m512i) __builtin_ia32_prolq512_mask ((__v8di) __A, __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -6978,7 +6979,7 @@ _mm512_ror_epi64 (__m512i __A, int __B) { return (__m512i) __builtin_ia32_prorq512_mask ((__v8di) __A, __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -7005,7 +7006,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_undefined_si512 (), \ + (__v16si)_mm512_undefined_epi32 (), \ (__mmask16)(-1))) #define _mm512_mask_rol_epi32(W, U, A, B) \ ((__m512i)__builtin_ia32_prold512_mask ((__v16si)(__m512i)(A), \ @@ -7020,7 +7021,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_undefined_si512 (), \ + (__v16si)_mm512_undefined_epi32 (), \ (__mmask16)(-1))) #define _mm512_mask_ror_epi32(W, U, A, B) \ ((__m512i)__builtin_ia32_prord512_mask ((__v16si)(__m512i)(A), \ @@ -7035,7 +7036,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_undefined_si512 (), \ + (__v8di)_mm512_undefined_epi32 (), \ (__mmask8)(-1))) #define _mm512_mask_rol_epi64(W, U, A, B) \ ((__m512i)__builtin_ia32_prolq512_mask ((__v8di)(__m512i)(A), \ @@ -7051,7 +7052,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_undefined_si512 (), \ + (__v8di)_mm512_undefined_epi32 (), \ (__mmask8)(-1))) #define _mm512_mask_ror_epi64(W, U, A, B) \ ((__m512i)__builtin_ia32_prorq512_mask ((__v8di)(__m512i)(A), \ @@ -7134,7 +7135,7 @@ _mm512_andnot_si512 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pandnd512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -7145,7 +7146,7 @@ _mm512_andnot_epi32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pandnd512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -7177,7 +7178,7 @@ _mm512_andnot_epi64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pandnq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -7275,7 +7276,7 @@ _mm512_unpackhi_epi32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_punpckhdq512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -7308,7 +7309,7 @@ _mm512_unpackhi_epi64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_punpckhqdq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -7340,7 +7341,7 @@ _mm512_unpacklo_epi32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_punpckldq512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -7373,7 +7374,7 @@ _mm512_unpacklo_epi64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_punpcklqdq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -8512,7 +8513,7 @@ _mm512_alignr_epi32 (__m512i __A, __m512i __B, const int __imm) return (__m512i) __builtin_ia32_alignd512_mask ((__v16si) __A, (__v16si) __B, __imm, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -8546,7 +8547,7 @@ _mm512_alignr_epi64 (__m512i __A, __m512i __B, const int __imm) return (__m512i) __builtin_ia32_alignq512_mask ((__v8di) __A, (__v8di) __B, __imm, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -8575,7 +8576,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)_mm512_undefined_si512 (),\ + (__v16si)(__m512i)(Y), (int)(C), (__v16si)_mm512_undefined_epi32 (),\ (__mmask16)-1)) #define _mm512_mask_alignr_epi32(W, U, X, Y, C) \ @@ -8590,7 +8591,7 @@ _mm512_maskz_alignr_epi64 (__mmask8 __U, __m512i __A, __m512i __B, #define _mm512_alignr_epi64(X, Y, C) \ ((__m512i)__builtin_ia32_alignq512_mask ((__v8di)(__m512i)(X), \ - (__v8di)(__m512i)(Y), (int)(C), (__v8di)_mm512_undefined_si512 (), \ + (__v8di)(__m512i)(Y), (int)(C), (__v8di)_mm512_undefined_epi32 (), \ (__mmask8)-1)) #define _mm512_mask_alignr_epi64(W, U, X, Y, C) \ @@ -9306,7 +9307,7 @@ extern __inline __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) _mm512_i32gather_epi32 (__m512i __index, int const *__addr, int __scale) { - __m512i v1_old = _mm512_undefined_si512 (); + __m512i v1_old = _mm512_undefined_epi32 (); __mmask16 mask = 0xFFFF; return (__m512i) __builtin_ia32_gathersiv16si ((__v16si) v1_old, @@ -9330,7 +9331,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_undefined_si512 (); + __m512i v1_old = _mm512_undefined_epi32 (); __mmask8 mask = 0xFF; return (__m512i) __builtin_ia32_gathersiv8di ((__v8di) v1_old, @@ -9379,7 +9380,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_undefined_si512 (); + __m512i v1_old = _mm512_undefined_epi32 (); __mmask8 mask = 0xFF; return (__m512i) __builtin_ia32_gatherdiv8di ((__v8di) v1_old, @@ -9591,7 +9592,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_undefined_si512 (), \ + (__m512i) __builtin_ia32_gathersiv16si ((__v16si)_mm512_undefined_epi32 (), \ (int const *)ADDR, \ (__v16si)(__m512i)INDEX, \ (__mmask16)0xFFFF, (int)SCALE) @@ -9603,7 +9604,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_undefined_si512 (), \ + (__m512i) __builtin_ia32_gathersiv8di ((__v8di)_mm512_undefined_epi32 (), \ (long long const *)ADDR, \ (__v8si)(__m256i)INDEX, \ (__mmask8)0xFF, (int)SCALE) @@ -9627,7 +9628,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_undefined_si512 (), \ + (__m512i) __builtin_ia32_gatherdiv8di ((__v8di)_mm512_undefined_epi32 (), \ (long long const *)ADDR, \ (__v8di)(__m512i)INDEX, \ (__mmask8)0xFF, (int)SCALE) @@ -10123,7 +10124,7 @@ _mm512_max_epi64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pmaxsq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -10154,7 +10155,7 @@ _mm512_min_epi64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pminsq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -10185,7 +10186,7 @@ _mm512_max_epu64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pmaxuq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -10216,7 +10217,7 @@ _mm512_min_epu64 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pminuq512_mask ((__v8di) __A, (__v8di) __B, (__v8di) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask8) -1); } @@ -10247,7 +10248,7 @@ _mm512_max_epi32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pmaxsd512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -10278,7 +10279,7 @@ _mm512_min_epi32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pminsd512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -10309,7 +10310,7 @@ _mm512_max_epu32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pmaxud512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -10340,7 +10341,7 @@ _mm512_min_epu32 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_pminud512_mask ((__v16si) __A, (__v16si) __B, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1); } @@ -11804,7 +11805,7 @@ _mm512_cvttps_epi32 (__m512 __A) { return (__m512i) __builtin_ia32_cvttps2dq512_mask ((__v16sf) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1, _MM_FROUND_CUR_DIRECTION); } @@ -11836,7 +11837,7 @@ _mm512_cvttps_epu32 (__m512 __A) { return (__m512i) __builtin_ia32_cvttps2udq512_mask ((__v16sf) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1, _MM_FROUND_CUR_DIRECTION); } @@ -11868,7 +11869,7 @@ _mm512_cvtps_epi32 (__m512 __A) { return (__m512i) __builtin_ia32_cvtps2dq512_mask ((__v16sf) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1, _MM_FROUND_CUR_DIRECTION); } @@ -11900,7 +11901,7 @@ _mm512_cvtps_epu32 (__m512 __A) { return (__m512i) __builtin_ia32_cvtps2udq512_mask ((__v16sf) __A, (__v16si) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask16) -1, _MM_FROUND_CUR_DIRECTION); } diff --git a/gcc/config/i386/avx512ifmaintrin.h b/gcc/config/i386/avx512ifmaintrin.h index b558981b2583..281aa64f2739 100644 --- a/gcc/config/i386/avx512ifmaintrin.h +++ b/gcc/config/i386/avx512ifmaintrin.h @@ -41,7 +41,7 @@ _mm512_madd52lo_epu64 (__m512i __X, __m512i __Y, __m512i __Z) return (__m512i) __builtin_ia32_vpmadd52luq512_mask ((__v8di) __X, (__v8di) __Y, (__v8di) __Z, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __m512i @@ -51,7 +51,7 @@ _mm512_madd52hi_epu64 (__m512i __X, __m512i __Y, __m512i __Z) return (__m512i) __builtin_ia32_vpmadd52huq512_mask ((__v8di) __X, (__v8di) __Y, (__v8di) __Z, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __m512i diff --git a/gcc/config/i386/avx512ifmavlintrin.h b/gcc/config/i386/avx512ifmavlintrin.h index 750eaff3ed64..ac37646eba56 100644 --- a/gcc/config/i386/avx512ifmavlintrin.h +++ b/gcc/config/i386/avx512ifmavlintrin.h @@ -41,7 +41,7 @@ _mm_madd52lo_epu64 (__m128i __X, __m128i __Y, __m128i __Z) return (__m128i) __builtin_ia32_vpmadd52luq128_mask ((__v2di) __X, (__v2di) __Y, (__v2di) __Z, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __m128i @@ -51,7 +51,7 @@ _mm_madd52hi_epu64 (__m128i __X, __m128i __Y, __m128i __Z) return (__m128i) __builtin_ia32_vpmadd52huq128_mask ((__v2di) __X, (__v2di) __Y, (__v2di) __Z, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __m256i @@ -61,7 +61,7 @@ _mm256_madd52lo_epu64 (__m256i __X, __m256i __Y, __m256i __Z) return (__m256i) __builtin_ia32_vpmadd52luq256_mask ((__v4di) __X, (__v4di) __Y, (__v4di) __Z, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __m256i @@ -71,7 +71,7 @@ _mm256_madd52hi_epu64 (__m256i __X, __m256i __Y, __m256i __Z) return (__m256i) __builtin_ia32_vpmadd52huq256_mask ((__v4di) __X, (__v4di) __Y, (__v4di) __Z, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __m128i diff --git a/gcc/config/i386/avx512vbmiintrin.h b/gcc/config/i386/avx512vbmiintrin.h index f93b13b47d29..7a14865dfbcc 100644 --- a/gcc/config/i386/avx512vbmiintrin.h +++ b/gcc/config/i386/avx512vbmiintrin.h @@ -62,7 +62,7 @@ _mm512_multishift_epi64_epi8 (__m512i __X, __m512i __Y) return (__m512i) __builtin_ia32_vpmultishiftqb512_mask ((__v64qi) __X, (__v64qi) __Y, (__v64qi) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask64) -1); } @@ -73,7 +73,7 @@ _mm512_permutexvar_epi8 (__m512i __A, __m512i __B) return (__m512i) __builtin_ia32_permvarqi512_mask ((__v64qi) __B, (__v64qi) __A, (__v64qi) - _mm512_undefined_si512 (), + _mm512_undefined_epi32 (), (__mmask64) -1); } @@ -108,8 +108,7 @@ _mm512_permutex2var_epi8 (__m512i __A, __m512i __I, __m512i __B) /* idx */ , (__v64qi) __A, (__v64qi) __B, - (__mmask64) - - 1); + (__mmask64) -1); } extern __inline __m512i diff --git a/gcc/config/i386/avx512vbmivlintrin.h b/gcc/config/i386/avx512vbmivlintrin.h index cab4e5c07c5f..f7af20e70837 100644 --- a/gcc/config/i386/avx512vbmivlintrin.h +++ b/gcc/config/i386/avx512vbmivlintrin.h @@ -173,8 +173,7 @@ _mm256_permutex2var_epi8 (__m256i __A, __m256i __I, __m256i __B) /* idx */ , (__v32qi) __A, (__v32qi) __B, - (__mmask32) - - 1); + (__mmask32) -1); } extern __inline __m256i @@ -224,8 +223,7 @@ _mm_permutex2var_epi8 (__m128i __A, __m128i __I, __m128i __B) /* idx */ , (__v16qi) __A, (__v16qi) __B, - (__mmask16) - - 1); + (__mmask16) -1); } extern __inline __m128i diff --git a/gcc/config/i386/avx512vlbwintrin.h b/gcc/config/i386/avx512vlbwintrin.h index 601dcdd91a10..9423101a90ad 100644 --- a/gcc/config/i386/avx512vlbwintrin.h +++ b/gcc/config/i386/avx512vlbwintrin.h @@ -575,8 +575,7 @@ _mm256_permutex2var_epi16 (__m256i __A, __m256i __I, __m256i __B) /* idx */ , (__v16hi) __A, (__v16hi) __B, - (__mmask16) - - 1); + (__mmask16) -1); } extern __inline __m256i @@ -626,8 +625,7 @@ _mm_permutex2var_epi16 (__m128i __A, __m128i __I, __m128i __B) /* idx */ , (__v8hi) __A, (__v8hi) __B, - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128i @@ -2009,7 +2007,7 @@ _mm256_cmpneq_epi8_mask (__m256i __X, __m256i __Y) { return (__mmask32) __builtin_ia32_cmpb256_mask ((__v32qi) __X, (__v32qi) __Y, 4, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2018,7 +2016,7 @@ _mm256_cmplt_epi8_mask (__m256i __X, __m256i __Y) { return (__mmask32) __builtin_ia32_cmpb256_mask ((__v32qi) __X, (__v32qi) __Y, 1, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2027,7 +2025,7 @@ _mm256_cmpge_epi8_mask (__m256i __X, __m256i __Y) { return (__mmask32) __builtin_ia32_cmpb256_mask ((__v32qi) __X, (__v32qi) __Y, 5, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -2036,7 +2034,7 @@ _mm256_cmple_epi8_mask (__m256i __X, __m256i __Y) { return (__mmask32) __builtin_ia32_cmpb256_mask ((__v32qi) __X, (__v32qi) __Y, 2, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask16 @@ -2045,7 +2043,7 @@ _mm256_cmpneq_epi16_mask (__m256i __X, __m256i __Y) { return (__mmask16) __builtin_ia32_cmpw256_mask ((__v16hi) __X, (__v16hi) __Y, 4, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2054,7 +2052,7 @@ _mm256_cmplt_epi16_mask (__m256i __X, __m256i __Y) { return (__mmask16) __builtin_ia32_cmpw256_mask ((__v16hi) __X, (__v16hi) __Y, 1, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2063,7 +2061,7 @@ _mm256_cmpge_epi16_mask (__m256i __X, __m256i __Y) { return (__mmask16) __builtin_ia32_cmpw256_mask ((__v16hi) __X, (__v16hi) __Y, 5, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2072,7 +2070,7 @@ _mm256_cmple_epi16_mask (__m256i __X, __m256i __Y) { return (__mmask16) __builtin_ia32_cmpw256_mask ((__v16hi) __X, (__v16hi) __Y, 2, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2081,7 +2079,7 @@ _mm_cmpneq_epu8_mask (__m128i __X, __m128i __Y) { return (__mmask16) __builtin_ia32_ucmpb128_mask ((__v16qi) __X, (__v16qi) __Y, 4, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2090,7 +2088,7 @@ _mm_cmplt_epu8_mask (__m128i __X, __m128i __Y) { return (__mmask16) __builtin_ia32_ucmpb128_mask ((__v16qi) __X, (__v16qi) __Y, 1, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2099,7 +2097,7 @@ _mm_cmpge_epu8_mask (__m128i __X, __m128i __Y) { return (__mmask16) __builtin_ia32_ucmpb128_mask ((__v16qi) __X, (__v16qi) __Y, 5, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2108,7 +2106,7 @@ _mm_cmple_epu8_mask (__m128i __X, __m128i __Y) { return (__mmask16) __builtin_ia32_ucmpb128_mask ((__v16qi) __X, (__v16qi) __Y, 2, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask8 @@ -2117,7 +2115,7 @@ _mm_cmpneq_epu16_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpw128_mask ((__v8hi) __X, (__v8hi) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -2126,7 +2124,7 @@ _mm_cmplt_epu16_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpw128_mask ((__v8hi) __X, (__v8hi) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -2135,7 +2133,7 @@ _mm_cmpge_epu16_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpw128_mask ((__v8hi) __X, (__v8hi) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -2144,7 +2142,7 @@ _mm_cmple_epu16_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpw128_mask ((__v8hi) __X, (__v8hi) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask16 @@ -2153,7 +2151,7 @@ _mm_cmpneq_epi8_mask (__m128i __X, __m128i __Y) { return (__mmask16) __builtin_ia32_cmpb128_mask ((__v16qi) __X, (__v16qi) __Y, 4, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2162,7 +2160,7 @@ _mm_cmplt_epi8_mask (__m128i __X, __m128i __Y) { return (__mmask16) __builtin_ia32_cmpb128_mask ((__v16qi) __X, (__v16qi) __Y, 1, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2171,7 +2169,7 @@ _mm_cmpge_epi8_mask (__m128i __X, __m128i __Y) { return (__mmask16) __builtin_ia32_cmpb128_mask ((__v16qi) __X, (__v16qi) __Y, 5, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -2180,7 +2178,7 @@ _mm_cmple_epi8_mask (__m128i __X, __m128i __Y) { return (__mmask16) __builtin_ia32_cmpb128_mask ((__v16qi) __X, (__v16qi) __Y, 2, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask8 @@ -2189,7 +2187,7 @@ _mm_cmpneq_epi16_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpw128_mask ((__v8hi) __X, (__v8hi) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -2198,7 +2196,7 @@ _mm_cmplt_epi16_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpw128_mask ((__v8hi) __X, (__v8hi) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -2207,7 +2205,7 @@ _mm_cmpge_epi16_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpw128_mask ((__v8hi) __X, (__v8hi) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -2216,7 +2214,7 @@ _mm_cmple_epi16_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpw128_mask ((__v8hi) __X, (__v8hi) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __m256i @@ -3609,7 +3607,7 @@ _mm256_cmpneq_epu8_mask (__m256i __X, __m256i __Y) { return (__mmask32) __builtin_ia32_ucmpb256_mask ((__v32qi) __X, (__v32qi) __Y, 4, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -3618,7 +3616,7 @@ _mm256_cmplt_epu8_mask (__m256i __X, __m256i __Y) { return (__mmask32) __builtin_ia32_ucmpb256_mask ((__v32qi) __X, (__v32qi) __Y, 1, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -3627,7 +3625,7 @@ _mm256_cmpge_epu8_mask (__m256i __X, __m256i __Y) { return (__mmask32) __builtin_ia32_ucmpb256_mask ((__v32qi) __X, (__v32qi) __Y, 5, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask32 @@ -3636,7 +3634,7 @@ _mm256_cmple_epu8_mask (__m256i __X, __m256i __Y) { return (__mmask32) __builtin_ia32_ucmpb256_mask ((__v32qi) __X, (__v32qi) __Y, 2, - (__mmask32) - 1); + (__mmask32) -1); } extern __inline __mmask16 @@ -3645,7 +3643,7 @@ _mm256_cmpneq_epu16_mask (__m256i __X, __m256i __Y) { return (__mmask16) __builtin_ia32_ucmpw256_mask ((__v16hi) __X, (__v16hi) __Y, 4, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -3654,7 +3652,7 @@ _mm256_cmplt_epu16_mask (__m256i __X, __m256i __Y) { return (__mmask16) __builtin_ia32_ucmpw256_mask ((__v16hi) __X, (__v16hi) __Y, 1, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -3663,7 +3661,7 @@ _mm256_cmpge_epu16_mask (__m256i __X, __m256i __Y) { return (__mmask16) __builtin_ia32_ucmpw256_mask ((__v16hi) __X, (__v16hi) __Y, 5, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline __mmask16 @@ -3672,7 +3670,7 @@ _mm256_cmple_epu16_mask (__m256i __X, __m256i __Y) { return (__mmask16) __builtin_ia32_ucmpw256_mask ((__v16hi) __X, (__v16hi) __Y, 2, - (__mmask16) - 1); + (__mmask16) -1); } extern __inline void diff --git a/gcc/config/i386/avx512vldqintrin.h b/gcc/config/i386/avx512vldqintrin.h index 7ccb62b45cbe..56e8513c78c7 100644 --- a/gcc/config/i386/avx512vldqintrin.h +++ b/gcc/config/i386/avx512vldqintrin.h @@ -389,8 +389,7 @@ _mm256_broadcast_f64x2 (__m128d __A) return (__m256d) __builtin_ia32_broadcastf64x2_256_mask ((__v2df) __A, (__v4df)_mm256_undefined_pd(), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256d @@ -421,8 +420,7 @@ _mm256_broadcast_i64x2 (__m128i __A) return (__m256i) __builtin_ia32_broadcasti64x2_256_mask ((__v2di) __A, (__v4di)_mm256_undefined_si256(), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256i @@ -452,8 +450,7 @@ _mm256_broadcast_f32x2 (__m128 __A) { return (__m256) __builtin_ia32_broadcastf32x2_256_mask ((__v4sf) __A, (__v8sf)_mm256_undefined_ps(), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256 @@ -482,8 +479,7 @@ _mm256_broadcast_i32x2 (__m128i __A) return (__m256i) __builtin_ia32_broadcasti32x2_256_mask ((__v4si) __A, (__v8si)_mm256_undefined_si256(), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256i @@ -514,8 +510,7 @@ _mm_broadcast_i32x2 (__m128i __A) return (__m128i) __builtin_ia32_broadcasti32x2_128_mask ((__v4si) __A, (__v4si)_mm_undefined_si128(), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128i @@ -1351,8 +1346,7 @@ _mm256_extractf64x2_pd (__m256d __A, const int __imm) __imm, (__v2df) _mm_setzero_pd (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128d @@ -1388,8 +1382,7 @@ _mm256_extracti64x2_epi64 (__m256i __A, const int __imm) __imm, (__v2di) _mm_setzero_di (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128i @@ -1743,8 +1736,7 @@ _mm256_inserti64x2 (__m256i __A, __m128i __B, const int __imm) __imm, (__v4di) _mm256_setzero_si256 (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256i @@ -1783,8 +1775,7 @@ _mm256_insertf64x2 (__m256d __A, __m128d __B, const int __imm) __imm, (__v4df) _mm256_setzero_pd (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256d diff --git a/gcc/config/i386/avx512vlintrin.h b/gcc/config/i386/avx512vlintrin.h index b995cecc8c04..36771f6ffe21 100644 --- a/gcc/config/i386/avx512vlintrin.h +++ b/gcc/config/i386/avx512vlintrin.h @@ -2698,8 +2698,7 @@ _mm256_broadcast_f32x4 (__m128 __A) { return (__m256) __builtin_ia32_broadcastf32x4_256_mask ((__v4sf) __A, (__v8sf)_mm256_undefined_pd (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256 @@ -2728,8 +2727,7 @@ _mm256_broadcast_i32x4 (__m128i __A) return (__m256i) __builtin_ia32_broadcasti32x4_256_mask ((__v4si) __A, (__v8si)_mm256_undefined_si256 (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256i @@ -6293,8 +6291,7 @@ _mm256_permutex2var_pd (__m256d __A, __m256i __I, __m256d __B) /* idx */ , (__v4df) __A, (__v4df) __B, - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256d @@ -6584,8 +6581,7 @@ _mm_permutex2var_pd (__m128d __A, __m128i __I, __m128d __B) /* idx */ , (__v2df) __A, (__v2df) __B, - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128d @@ -8259,8 +8255,7 @@ _mm256_conflict_epi64 (__m256i __A) return (__m256i) __builtin_ia32_vpconflictdi_256_mask ((__v4di) __A, (__v4di) _mm256_setzero_si256 (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256i @@ -8291,8 +8286,7 @@ _mm256_conflict_epi32 (__m256i __A) return (__m256i) __builtin_ia32_vpconflictsi_256_mask ((__v8si) __A, (__v8si) _mm256_setzero_si256 (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256i @@ -8381,8 +8375,7 @@ _mm_conflict_epi64 (__m128i __A) return (__m128i) __builtin_ia32_vpconflictdi_128_mask ((__v2di) __A, (__v2di) _mm_setzero_di (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128i @@ -8413,8 +8406,7 @@ _mm_conflict_epi32 (__m128i __A) return (__m128i) __builtin_ia32_vpconflictsi_128_mask ((__v4si) __A, (__v4si) _mm_setzero_si128 (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128i @@ -9291,8 +9283,7 @@ _mm256_inserti32x4 (__m256i __A, __m128i __B, const int __imm) __imm, (__v8si) _mm256_setzero_si256 (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m256i @@ -9367,8 +9358,7 @@ _mm256_extracti32x4_epi32 (__m256i __A, const int __imm) __imm, (__v4si) _mm_setzero_si128 (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128i @@ -9404,8 +9394,7 @@ _mm256_extractf32x4_ps (__m256 __A, const int __imm) __imm, (__v4sf) _mm_setzero_ps (), - (__mmask8) - - 1); + (__mmask8) -1); } extern __inline __m128 @@ -11797,7 +11786,7 @@ _mm256_cmpneq_epu32_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_ucmpd256_mask ((__v8si) __X, (__v8si) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11815,7 +11804,7 @@ _mm256_cmplt_epu32_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_ucmpd256_mask ((__v8si) __X, (__v8si) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11833,7 +11822,7 @@ _mm256_cmpge_epu32_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_ucmpd256_mask ((__v8si) __X, (__v8si) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11851,7 +11840,7 @@ _mm256_cmple_epu32_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_ucmpd256_mask ((__v8si) __X, (__v8si) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11869,7 +11858,7 @@ _mm256_cmpneq_epu64_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_ucmpq256_mask ((__v4di) __X, (__v4di) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11887,7 +11876,7 @@ _mm256_cmplt_epu64_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_ucmpq256_mask ((__v4di) __X, (__v4di) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11905,7 +11894,7 @@ _mm256_cmpge_epu64_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_ucmpq256_mask ((__v4di) __X, (__v4di) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11923,7 +11912,7 @@ _mm256_cmple_epu64_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_ucmpq256_mask ((__v4di) __X, (__v4di) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11941,7 +11930,7 @@ _mm256_cmpneq_epi32_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_cmpd256_mask ((__v8si) __X, (__v8si) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11959,7 +11948,7 @@ _mm256_cmplt_epi32_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_cmpd256_mask ((__v8si) __X, (__v8si) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11977,7 +11966,7 @@ _mm256_cmpge_epi32_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_cmpd256_mask ((__v8si) __X, (__v8si) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -11995,7 +11984,7 @@ _mm256_cmple_epi32_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_cmpd256_mask ((__v8si) __X, (__v8si) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12013,7 +12002,7 @@ _mm256_cmpneq_epi64_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_cmpq256_mask ((__v4di) __X, (__v4di) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12031,7 +12020,7 @@ _mm256_cmplt_epi64_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_cmpq256_mask ((__v4di) __X, (__v4di) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12049,7 +12038,7 @@ _mm256_cmpge_epi64_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_cmpq256_mask ((__v4di) __X, (__v4di) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12067,7 +12056,7 @@ _mm256_cmple_epi64_mask (__m256i __X, __m256i __Y) { return (__mmask8) __builtin_ia32_cmpq256_mask ((__v4di) __X, (__v4di) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12085,7 +12074,7 @@ _mm_cmpneq_epu32_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpd128_mask ((__v4si) __X, (__v4si) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12103,7 +12092,7 @@ _mm_cmplt_epu32_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpd128_mask ((__v4si) __X, (__v4si) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12121,7 +12110,7 @@ _mm_cmpge_epu32_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpd128_mask ((__v4si) __X, (__v4si) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12139,7 +12128,7 @@ _mm_cmple_epu32_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpd128_mask ((__v4si) __X, (__v4si) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12157,7 +12146,7 @@ _mm_cmpneq_epu64_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpq128_mask ((__v2di) __X, (__v2di) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12175,7 +12164,7 @@ _mm_cmplt_epu64_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpq128_mask ((__v2di) __X, (__v2di) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12193,7 +12182,7 @@ _mm_cmpge_epu64_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpq128_mask ((__v2di) __X, (__v2di) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12211,7 +12200,7 @@ _mm_cmple_epu64_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_ucmpq128_mask ((__v2di) __X, (__v2di) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12229,7 +12218,7 @@ _mm_cmpneq_epi32_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpd128_mask ((__v4si) __X, (__v4si) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12247,7 +12236,7 @@ _mm_cmplt_epi32_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpd128_mask ((__v4si) __X, (__v4si) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12265,7 +12254,7 @@ _mm_cmpge_epi32_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpd128_mask ((__v4si) __X, (__v4si) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12283,7 +12272,7 @@ _mm_cmple_epi32_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpd128_mask ((__v4si) __X, (__v4si) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12301,7 +12290,7 @@ _mm_cmpneq_epi64_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpq128_mask ((__v2di) __X, (__v2di) __Y, 4, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12319,7 +12308,7 @@ _mm_cmplt_epi64_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpq128_mask ((__v2di) __X, (__v2di) __Y, 1, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12337,7 +12326,7 @@ _mm_cmpge_epi64_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpq128_mask ((__v2di) __X, (__v2di) __Y, 5, - (__mmask8) - 1); + (__mmask8) -1); } extern __inline __mmask8 @@ -12355,7 +12344,7 @@ _mm_cmple_epi64_mask (__m128i __X, __m128i __Y) { return (__mmask8) __builtin_ia32_cmpq128_mask ((__v2di) __X, (__v2di) __Y, 2, - (__mmask8) - 1); + (__mmask8) -1); } #else diff --git a/gcc/config/i386/i386.md b/gcc/config/i386/i386.md index da4af3fcd78b..42c5da9e04df 100644 --- a/gcc/config/i386/i386.md +++ b/gcc/config/i386/i386.md @@ -2974,7 +2974,7 @@ (match_operand:TF 1 "general_operand" "C ,xm,x,*roF,*rC"))] "(TARGET_64BIT || TARGET_SSE) && !(MEM_P (operands[0]) && MEM_P (operands[1])) - && (!can_create_pseudo_p () + && (lra_in_progress || reload_completed || (ix86_cmodel == CM_MEDIUM || ix86_cmodel == CM_LARGE) || GET_CODE (operands[1]) != CONST_DOUBLE || (optimize_function_for_size_p (cfun) @@ -3044,7 +3044,7 @@ (match_operand:XF 1 "general_operand" "fm,f,G,roF,r , *roF,*r,F ,C"))] "!(MEM_P (operands[0]) && MEM_P (operands[1])) - && (!can_create_pseudo_p () + && (lra_in_progress || reload_completed || (ix86_cmodel == CM_MEDIUM || ix86_cmodel == CM_LARGE) || GET_CODE (operands[1]) != CONST_DOUBLE || (optimize_function_for_size_p (cfun) @@ -3098,7 +3098,7 @@ (match_operand:DF 1 "general_operand" "Yf*fm,Yf*f,G ,roF,r ,*roF,*r,F ,rm,rC,C ,F ,C,v,m,v,C ,*x,m ,*x,Yj,r"))] "!(MEM_P (operands[0]) && MEM_P (operands[1])) - && (!can_create_pseudo_p () + && (lra_in_progress || reload_completed || (ix86_cmodel == CM_MEDIUM || ix86_cmodel == CM_LARGE) || GET_CODE (operands[1]) != CONST_DOUBLE || (optimize_function_for_size_p (cfun) @@ -3281,7 +3281,7 @@ (match_operand:SF 1 "general_operand" "Yf*fm,Yf*f,G ,rmF,rF,C,v,m,v,Yj,r ,*y ,m ,*y,*Yn,r"))] "!(MEM_P (operands[0]) && MEM_P (operands[1])) - && (!can_create_pseudo_p () + && (lra_in_progress || reload_completed || (ix86_cmodel == CM_MEDIUM || ix86_cmodel == CM_LARGE) || GET_CODE (operands[1]) != CONST_DOUBLE || (optimize_function_for_size_p (cfun) diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog index 3457b0da5ee4..0bb9a0e8052c 100644 --- a/gcc/testsuite/ChangeLog +++ b/gcc/testsuite/ChangeLog @@ -1,3 +1,11 @@ +2016-08-22 Uros Bizjak + + Backport from mainline + 2016-08-14 Uros Bizjak + + PR target/76342 + * gcc.target/i386/pr76342.c: New test. + 2016-08-13 Thomas Koenig Backport from trunk diff --git a/gcc/testsuite/gcc.target/i386/pr76342.c b/gcc/testsuite/gcc.target/i386/pr76342.c new file mode 100644 index 000000000000..d492b00c1aa1 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr76342.c @@ -0,0 +1,11 @@ +/* PR target/76342 */ +/* { dg-do compile } */ +/* { dg-options "-mavx512f" } */ + +#include + +__m512i +test() +{ + return _mm512_undefined_epi32 (); +}