[PATCH v3 7/7][X86] Add Sub-byte element extration and Symmetric-signed saturation narrow support.
Dipesh Sharma <[email protected]>
| Newsgroups | gmane.comp.gcc.patches |
|---|---|
| Message-ID | <[email protected]> |
Hi, Addressed review comments from Haochen Jiang and added more -mavx10v2aux and corresponding constant builtin/intrin test defines. bootstraped and regtested on x86_64-linux-gnu. ok for trunk ? gcc/ChangeLog: * config/i386/avx10v2auxintrin.h (_mm_cvtss_epi32_epi8): New intrin. (_mm_mask_cvtss_epi32_epi8): Ditto. (_mm_maskz_cvtss_epi32_epi8): Ditto. (_mm_mask_cvtss_epi32_storeu_epi8): Ditto. (_mm256_cvtss_epi32_epi8): Ditto. (_mm256_mask_cvtss_epi32_epi8): Ditto. (_mm256_maskz_cvtss_epi32_epi8): Ditto. (_mm256_mask_cvtss_epi32_storeu_epi8): Ditto. (_mm512_cvtss_epi32_epi8): Ditto. (_mm512_mask_cvtss_epi32_epi8): Ditto. (_mm512_maskz_cvtss_epi32_epi8): Ditto. (_mm512_mask_cvtss_epi32_storeu_epi8): Ditto. (_mm_unpack_epi8): Ditto. (_mm_mask_unpack_epi8): Ditto. (_mm_maskz_unpack_epi8): Ditto. (_mm256_unpack_epi8): Ditto. (_mm256_mask_unpack_epi8): Ditto. (_mm256_maskz_unpack_epi8): Ditto. (_mm512_unpack_epi8): Ditto. (_mm512_mask_unpack_epi8): Ditto. (_mm512_maskz_unpack_epi8): Ditto. * config/i386/i386-builtin-types.def: New function types. * config/i386/i386-builtin.def (BDESC): New builtins. * config/i386/i386-expand.cc (ix86_expand_args_builtin): Handle new function types and reserved immediate check. * config/i386/sse.md (vunpackb<mode><mask_name>): New. (avx10v2aux_sym_truncatev4siv4qi2): Ditto. (*avx10v2aux_sym_truncatev4siv4qi2): Ditto. (avx10v2aux_sym_truncatev8siv8qi2): Ditto. (*avx10v2aux_sym_truncatev8siv8qi2): Ditto. (avx10v2aux_sym_truncatev4siv4qi2_mask): Ditto. (*avx10v2aux_sym_truncatev4siv4qi2_mask): Ditto. (avx10v2aux_sym_truncatev8siv8qi2_mask): Ditto. (*avx10v2aux_sym_truncatev8siv8qi2_mask): Ditto. (*avx10v2aux_sym_truncatev16siv16qi2): Ditto. (avx10v2aux_sym_truncatev16siv16qi2_mask): Ditto. (avx10v2aux_sym_truncatev16siv16qi2_mask_store): Ditto. (*avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_store_1): Ditto. (*avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_store_2): Ditto. (avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_mask_store_1): Ditto. (avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_mask_store_2): Ditto. gcc/testsuite/ChangeLog: * g++.dg/other/i386-2.C: Add tests for avx10v2aux. * g++.dg/other/i386-3.C: Likewise. * gcc.target/i386/avx-1.c: Likewise. * gcc.target/i386/funcspec-56.inc: Likewise. * gcc.target/i386/sse-12.c: Likewise. * gcc.target/i386/sse-13.c: Likewise. * gcc.target/i386/sse-14.c: Likewise. * gcc.target/i386/sse-22.c: Likewise. * gcc.target/i386/sse-23.c: Likewise. * lib/target-supports.exp: Add more checks for avx10v2aux. * gcc.target/i386/avx10v2aux-convert-1i.c: New test. * gcc.target/i386/avx10v2aux-convert-1j.c: New test. * gcc.target/i386/avx10v2aux-convert-1k.c: New test. * gcc.target/i386/avx10v2aux-convert-1l.c: New test. Co-authored-by: Venkataramanan Kumar <[email protected]> Co-authored-by: Haochen Jiang <[email protected]> --- gcc/config/i386/avx10v2auxintrin.h | 287 ++++++++++++++++++ gcc/config/i386/i386-builtin-types.def | 3 + gcc/config/i386/i386-builtin.def | 13 + gcc/config/i386/i386-expand.cc | 21 ++ gcc/config/i386/sse.md | 238 +++++++++++++++ gcc/testsuite/g++.dg/other/i386-2.C | 4 +- gcc/testsuite/g++.dg/other/i386-3.C | 4 +- gcc/testsuite/gcc.target/i386/avx-1.c | 7 +- .../gcc.target/i386/avx10v2aux-convert-1i.c | 36 +++ .../gcc.target/i386/avx10v2aux-convert-1j.c | 43 +++ .../gcc.target/i386/avx10v2aux-convert-1k.c | 29 ++ .../gcc.target/i386/avx10v2aux-convert-1l.c | 27 ++ gcc/testsuite/gcc.target/i386/funcspec-56.inc | 2 + gcc/testsuite/gcc.target/i386/sse-12.c | 2 +- gcc/testsuite/gcc.target/i386/sse-13.c | 7 +- gcc/testsuite/gcc.target/i386/sse-14.c | 13 +- gcc/testsuite/gcc.target/i386/sse-22.c | 17 +- gcc/testsuite/gcc.target/i386/sse-23.c | 9 +- gcc/testsuite/lib/target-supports.exp | 3 + 19 files changed, 752 insertions(+), 13 deletions(-) create mode 100644 gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1i.c create mode 100644 gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1j.c create mode 100644 gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1k.c create mode 100644 gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1l.c diff --git a/gcc/config/i386/avx10v2auxintrin.h b/gcc/config/i386/avx10v2auxintrin.h index bab9cb1475b..f15343f2389 100644 --- a/gcc/config/i386/avx10v2auxintrin.h +++ b/gcc/config/i386/avx10v2auxintrin.h @@ -1566,6 +1566,293 @@ _mm512_maskz_cvthf6_hf8 (__mmask64 __U, __m512i __A) (__mmask64) __U); } +// VPMOVSSDB - 128-bit + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm_cvtss_epi32_epi8 (__m128i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb128_mask ((__v4si) __A, + (__v16qi) + _mm_undefined_si128 (), + (__mmask8) -1); +} + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm_mask_cvtss_epi32_epi8 (__m128i __W, __mmask8 __U, __m128i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb128_mask ((__v4si) __A, + (__v16qi) __W, + (__mmask8) __U); +} + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm_maskz_cvtss_epi32_epi8 (__mmask8 __U, __m128i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb128_mask ((__v4si) __A, + (__v16qi) + _mm_setzero_si128 (), + (__mmask8) __U); +} + +extern __inline void +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm_mask_cvtss_epi32_storeu_epi8 (void * __P, __mmask8 __U, __m128i __A) +{ + __builtin_ia32_vpmovssdb128mem_mask ((unsigned int *) __P, + (__v4si) __A, + (__mmask8) __U); +} + +// VPMOVSSDB - 256-bit + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm256_cvtss_epi32_epi8 (__m256i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb256_mask ((__v8si) __A, + (__v16qi) + _mm_undefined_si128 (), + (__mmask8) -1); +} + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm256_mask_cvtss_epi32_epi8 (__m128i __W, __mmask8 __U, __m256i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb256_mask ((__v8si) __A, + (__v16qi) __W, + (__mmask8) __U); +} + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm256_maskz_cvtss_epi32_epi8 (__mmask8 __U, __m256i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb256_mask ((__v8si) __A, + (__v16qi) + _mm_setzero_si128 (), + (__mmask8) __U); +} + +extern __inline void +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm256_mask_cvtss_epi32_storeu_epi8 (void * __P, __mmask8 __U, __m256i __A) +{ + __builtin_ia32_vpmovssdb256mem_mask ((unsigned long long *) __P, + (__v8si) __A, + (__mmask8) __U); +} + +// VPMOVSSDB - 512-bit + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm512_cvtss_epi32_epi8 (__m512i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb512_mask ((__v16si) __A, + (__v16qi) + _mm_undefined_si128 (), + (__mmask16) -1); +} + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm512_mask_cvtss_epi32_epi8 (__m128i __W, __mmask16 __U, __m512i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb512_mask ((__v16si) __A, + (__v16qi) __W, + (__mmask16) __U); +} + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm512_maskz_cvtss_epi32_epi8 (__mmask16 __U, __m512i __A) +{ + return (__m128i) __builtin_ia32_vpmovssdb512_mask ((__v16si) __A, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) __U); +} + +extern __inline void +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm512_mask_cvtss_epi32_storeu_epi8 (void * __P, __mmask16 __U, __m512i __A) +{ + __builtin_ia32_vpmovssdb512mem_mask ((__v16qi *) __P, + (__v16si) __A, + (__mmask16) __U); +} + +// VUNPACKB - 128-bit +#ifdef __OPTIMIZE__ +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm_unpack_epi8 (__m128i __A, const int __B) +{ + return (__m128i) __builtin_ia32_vunpackb128_mask ((__v16qi) __A, + (const int) __B, + (__v16qi) + _mm_undefined_si128 (), + (__mmask16) -1); +} + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm_mask_unpack_epi8 (__m128i __W, __mmask16 __U, + __m128i __A, const int __B) +{ + return (__m128i) __builtin_ia32_vunpackb128_mask ((__v16qi) __A, + (const int) __B, + (__v16qi) __W, + (__mmask16) __U); +} + +extern __inline __m128i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm_maskz_unpack_epi8 (__mmask16 __U, __m128i __A, const int __B) +{ + return (__m128i) __builtin_ia32_vunpackb128_mask ((__v16qi) __A, + (const int) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) __U); +} + +// VUNPACKB - 256-bit + +extern __inline __m256i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm256_unpack_epi8 (__m256i __A, const int __B) +{ + return (__m256i) __builtin_ia32_vunpackb256_mask ((__v32qi) __A, + (const int) __B, + (__v32qi) + _mm256_undefined_si256 (), + (__mmask32) -1); +} + +extern __inline __m256i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm256_mask_unpack_epi8 (__m256i __W, __mmask32 __U, + __m256i __A, const int __B) +{ + return (__m256i) __builtin_ia32_vunpackb256_mask ((__v32qi) __A, + (const int) __B, + (__v32qi) __W, + (__mmask32) __U); +} + +extern __inline __m256i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm256_maskz_unpack_epi8 (__mmask32 __U, __m256i __A, const int __B) +{ + return (__m256i) __builtin_ia32_vunpackb256_mask ((__v32qi) __A, + (const int) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) __U); +} + +// VUNPACKB - 512-bit + +extern __inline __m512i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm512_unpack_epi8 (__m512i __A, const int __B) +{ + return (__m512i) __builtin_ia32_vunpackb512_mask ((__v64qi) __A, + (const int) __B, + (__v64qi) + _mm512_undefined_si512 (), + (__mmask64) -1); +} + +extern __inline __m512i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm512_mask_unpack_epi8 (__m512i __W, __mmask64 __U, __m512i __A, + const int __B) +{ + return (__m512i) __builtin_ia32_vunpackb512_mask ((__v64qi) __A, + (const int) __B, + (__v64qi) __W, + (__mmask64) __U); +} + +extern __inline __m512i +__attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) +_mm512_maskz_unpack_epi8 (__mmask64 __U, __m512i __A, const int __B) +{ + return (__m512i) __builtin_ia32_vunpackb512_mask ((__v64qi) __A, + (const int) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) __U); +} + +#else +#define _mm_unpack_epi8(A, imm) \ + ((__m128i) __builtin_ia32_vunpackb128_mask ((__v16qi)(__m128i)(A), \ + (int)(imm), \ + (__v16qi)(__m128i) \ + (_mm_undefined_si128 ()), \ + (__mmask16)(-1))) + +#define _mm_mask_unpack_epi8(W, U, A, imm) \ + ((__m128i) __builtin_ia32_vunpackb128_mask ((__v16qi)(__m128i)(A), \ + (int)(imm), \ + (__v16qi)(__m128i)(W), \ + (__mmask16)(U))) + +#define _mm_maskz_unpack_epi8(U, A, imm) \ + ((__m128i) __builtin_ia32_vunpackb128_mask ((__v16qi)(__m128i)(A), \ + (int)(imm), \ + (__v16qi)(__m128i) \ + (_mm_undefined_si128 ()), \ + (__mmask16)(U))) + +#define _mm256_unpack_epi8(A, imm) \ + ((__m256i) __builtin_ia32_vunpackb256_mask ((__v32qi)(__m256i)(A), \ + (int)(imm), \ + (__v32qi)(__m256i) \ + (_mm256_undefined_si256 ()), \ + (__mmask32)(-1))) + +#define _mm256_mask_unpack_epi8(W, U, A, imm) \ + ((__m256i) __builtin_ia32_vunpackb256_mask ((__v32qi)(__m256i)(A), \ + (int)(imm), \ + (__v32qi)(__m256i)(W), \ + (__mmask32)(U))) + +#define _mm256_maskz_unpack_epi8(U, A, imm) \ + ((__m256i) __builtin_ia32_vunpackb256_mask ((__v32qi)(__m256i)(A), \ + (int)(imm), \ + (__v32qi)(__m256i) \ + (_mm256_undefined_si256 ()), \ + (__mmask32)(U))) + +#define _mm512_unpack_epi8(A, imm) \ + ((__m512i) __builtin_ia32_vunpackb512_mask ((__v64qi)(__m512i)(A), \ + (int)(imm), \ + (__v64qi)(__m512i) \ + (_mm512_undefined_si512 ()), \ + (__mmask64)(-1))) + +#define _mm512_mask_unpack_epi8(W, U, A, imm) \ + ((__m512i) __builtin_ia32_vunpackb512_mask ((__v64qi)(__m512i)(A), \ + (int)(imm), \ + (__v64qi)(__m512i)(W), \ + (__mmask64)(U))) + +#define _mm512_maskz_unpack_epi8(U, A, imm) \ + ((__m512i) __builtin_ia32_vunpackb512_mask ((__v64qi)(__m512i)(A), \ + (int)(imm), \ + (__v64qi)(__m512i) \ + (_mm512_undefined_si512 ()), \ + (__mmask64)(U))) +#endif + #ifdef __DISABLE_AVX10V2AUX__ #undef __DISABLE_AVX10V2AUX__ #pragma GCC pop_options diff --git a/gcc/config/i386/i386-builtin-types.def b/gcc/config/i386/i386-builtin-types.def index ade9b3a67e2..4083453ce3e 100644 --- a/gcc/config/i386/i386-builtin-types.def +++ b/gcc/config/i386/i386-builtin-types.def @@ -1487,6 +1487,9 @@ DEF_FUNCTION_TYPE (V16SF, V16QI, V16SF, UHI) DEF_FUNCTION_TYPE (V16QI, V32QI) DEF_FUNCTION_TYPE (V32QI, V64QI) DEF_FUNCTION_TYPE (V64QI, V32QI, V64QI, UDI) +DEF_FUNCTION_TYPE (V16QI, V16QI, INT, V16QI, UHI) +DEF_FUNCTION_TYPE (V32QI, V32QI, INT, V32QI, USI) +DEF_FUNCTION_TYPE (V64QI, V64QI, INT, V64QI, UDI) # SM4 builtins diff --git a/gcc/config/i386/i386-builtin.def b/gcc/config/i386/i386-builtin.def index ad963e9011b..84f23239326 100644 --- a/gcc/config/i386/i386-builtin.def +++ b/gcc/config/i386/i386-builtin.def @@ -523,6 +523,12 @@ BDESC (OPTION_MASK_ISA_64BIT, OPTION_MASK_ISA2_MOVRS | OPTION_MASK_ISA2_AVX10_2, BDESC (OPTION_MASK_ISA_64BIT, OPTION_MASK_ISA2_MOVRS | OPTION_MASK_ISA2_AVX10_2, CODE_FOR_avx10_2_vmovrsqv2di_mask, "__builtin_ia32_vmovrsq128_mask", IX86_BUILTIN_VMOVRSQ_128, UNKNOWN, (int) V2DI_FTYPE_PCV2DI_V2DI_UQI) BDESC (OPTION_MASK_ISA_64BIT, OPTION_MASK_ISA2_MOVRS | OPTION_MASK_ISA2_AVX10_2, CODE_FOR_avx10_2_vmovrswv8hi_mask, "__builtin_ia32_vmovrsw128_mask", IX86_BUILTIN_VMOVRSW_128, UNKNOWN, (int) V8HI_FTYPE_PCV8HI_V8HI_UQI) +/* AVX10V2AUX. */ +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_avx10v2aux_sym_truncatev4siv4qi2_mask_store_2, "__builtin_ia32_vpmovssdb128mem_mask", IX86_BUILTIN_VPMOVSSDB128_MEM, UNKNOWN, (int) VOID_FTYPE_PUSI_V4SI_UQI) +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_avx10v2aux_sym_truncatev8siv8qi2_mask_store_2, "__builtin_ia32_vpmovssdb256mem_mask", IX86_BUILTIN_VPMOVSSDB256_MEM, UNKNOWN, (int) VOID_FTYPE_PUDI_V8SI_UQI) +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_avx10v2aux_sym_truncatev16siv16qi2_mask_store, "__builtin_ia32_vpmovssdb512mem_mask", IX86_BUILTIN_VPMOVSSDB512_MEM, UNKNOWN, (int) VOID_FTYPE_PV16QI_V16SI_UHI) + + BDESC_END (SPECIAL_ARGS, PURE_ARGS) /* AVX */ @@ -3427,6 +3433,13 @@ BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_vcvtbf62hf8v64qi_mask, "__builti BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_vcvthf62hf8v16qi_mask, "__builtin_ia32_vcvthf62hf8128_mask", IX86_BUILTIN_VCVTHF62HF8128_MASK, UNKNOWN, (int) V16QI_FTYPE_V16QI_V16QI_UHI) BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_vcvthf62hf8v32qi_mask, "__builtin_ia32_vcvthf62hf8256_mask", IX86_BUILTIN_VCVTHF62HF8256_MASK, UNKNOWN, (int) V32QI_FTYPE_V32QI_V32QI_USI) BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_vcvthf62hf8v64qi_mask, "__builtin_ia32_vcvthf62hf8512_mask", IX86_BUILTIN_VCVTHF62HF8512_MASK, UNKNOWN, (int) V64QI_FTYPE_V64QI_V64QI_UDI) +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_vunpackbv16qi_mask, "__builtin_ia32_vunpackb128_mask", IX86_BUILTIN_VUNPACKB128_MASK, UNKNOWN, (int) V16QI_FTYPE_V16QI_INT_V16QI_UHI) +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_vunpackbv32qi_mask, "__builtin_ia32_vunpackb256_mask", IX86_BUILTIN_VUNPACKB256_MASK, UNKNOWN, (int) V32QI_FTYPE_V32QI_INT_V32QI_USI) +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_vunpackbv64qi_mask, "__builtin_ia32_vunpackb512_mask", IX86_BUILTIN_VUNPACKB512_MASK, UNKNOWN, (int) V64QI_FTYPE_V64QI_INT_V64QI_UDI) +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_avx10v2aux_sym_truncatev4siv4qi2_mask, "__builtin_ia32_vpmovssdb128_mask", IX86_BUILTIN_VPMOVSSDB128_MASK, UNKNOWN, (int) V16QI_FTYPE_V4SI_V16QI_UQI) +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_avx10v2aux_sym_truncatev8siv8qi2_mask, "__builtin_ia32_vpmovssdb256_mask", IX86_BUILTIN_VPMOVSSDB256_MASK, UNKNOWN, (int) V16QI_FTYPE_V8SI_V16QI_UQI) +BDESC (0, OPTION_MASK_ISA2_AVX10V2AUX, CODE_FOR_avx10v2aux_sym_truncatev16siv16qi2_mask, "__builtin_ia32_vpmovssdb512_mask", IX86_BUILTIN_VPMOVSSDB512_MASK, UNKNOWN, (int) V16QI_FTYPE_V16SI_V16QI_UHI) + /* Builtins with rounding support. */ BDESC_END (ARGS, ROUND_ARGS) diff --git a/gcc/config/i386/i386-expand.cc b/gcc/config/i386/i386-expand.cc index fb4224af0da..7971ddce080 100644 --- a/gcc/config/i386/i386-expand.cc +++ b/gcc/config/i386/i386-expand.cc @@ -13322,6 +13322,9 @@ ix86_expand_args_builtin (const struct builtin_description *d, case V4DF_FTYPE_V8DF_INT_V4DF_UQI: case V4SF_FTYPE_V16SF_INT_V4SF_UQI: case V8DI_FTYPE_V8DI_INT_V8DI_UQI: + case V16QI_FTYPE_V16QI_INT_V16QI_UHI: + case V32QI_FTYPE_V32QI_INT_V32QI_USI: + case V64QI_FTYPE_V64QI_INT_V64QI_UDI: nargs = 4; mask_pos = 2; nargs_constant = 1; @@ -13453,6 +13456,8 @@ ix86_expand_args_builtin (const struct builtin_description *d, else if ((mask_pos && (nargs - i - mask_pos) == nargs_constant) || (!mask_pos && (nargs - i) <= nargs_constant)) { + + if (!match) switch (icode) { @@ -13592,6 +13597,22 @@ ix86_expand_args_builtin (const struct builtin_description *d, } return const0_rtx; } + if ((icode == CODE_FOR_vunpackbv16qi_mask + || icode == CODE_FOR_vunpackbv32qi_mask + || icode == CODE_FOR_vunpackbv64qi_mask) + && CONST_INT_P (op)) + { + char val = INTVAL (op); + if ((val & 0xc0) + || (!(val & 0x18)) + || ((val & 0x02) && ((val & 0x1c) != 0x08)) + || ((val & 0x01) && (((val & 0x1c) >> 2) > 0x4))) + { + error ("the last argument must not use reserved value " + "immediate"); + return const0_rtx; + } + } } else { diff --git a/gcc/config/i386/sse.md b/gcc/config/i386/sse.md index bf4c4505601..326d22a6d89 100644 --- a/gcc/config/i386/sse.md +++ b/gcc/config/i386/sse.md @@ -279,6 +279,8 @@ UNSPEC_VCVTHF82HF6S UNSPEC_VCVTBF62HF8 UNSPEC_VCVTHF62HF8 + UNSPEC_VUNPACKB + UNSPEC_VPMOVSSDB ]) (define_c_enum "unspecv" [ @@ -34683,3 +34685,239 @@ "vcvt<convertfp62hf8>\t{%1, %0<mask_operand2>|%0<mask_operand2>, %1}" [(set_attr "prefix" "evex") (set_attr "mode" "<sseinsnmode>")]) + +;; VUNPACKB - Sub-byte element extraction + +(define_insn "vunpackb<mode><mask_name>" + [(set (match_operand:VI1_AVX512VL 0 "register_operand" "=v") + (unspec:VI1_AVX512VL + [(match_operand:VI1_AVX512VL 1 "nonimmediate_operand" "vm") + (match_operand:QI 2 "const_0_to_255_operand")] + UNSPEC_VUNPACKB))] + "TARGET_AVX10V2AUX" + "vunpackb\t{%2, %1, %0<mask_operand3>|%0<mask_operand3>, %1, %2}" + [(set_attr "prefix" "evex") + (set_attr "mode" "<sseinsnmode>")]) + +;; VPMOVSSDB - Symmetric signed saturation narrow (32-bit to 8-bit) + +(define_mode_attr pmovss_mem_dest + [(V4SI "SI") (V8SI "DI")]) + +(define_mode_attr pmovss_sel_vec + [(V4SI "V4SI") (V8SI "V2DI")]) + +(define_expand "avx10v2aux_sym_truncatev4siv4qi2" + [(set (match_operand:V16QI 0 "nonimmediate_operand") + (vec_concat:V16QI + (unspec:V4QI + [(match_operand:V4SI 1 "register_operand")] + UNSPEC_VPMOVSSDB) + (match_dup 2)))] + "TARGET_AVX10V2AUX" + "operands[2] = CONST0_RTX (V12QImode);") + +(define_insn "*avx10v2aux_sym_truncatev4siv4qi2" + [(set (match_operand:V16QI 0 "register_operand" "=v") + (vec_concat:V16QI + (unspec:V4QI + [(match_operand:V4SI 1 "register_operand" "v")] + UNSPEC_VPMOVSSDB) + (match_operand:V12QI 2 "const0_operand")))] + "TARGET_AVX10V2AUX" + "vpmovssdb\t{%1, %0|%0, %1}" + [(set_attr "type" "ssemov") + (set_attr "prefix" "evex") + (set_attr "mode" "TI")]) + +(define_expand "avx10v2aux_sym_truncatev8siv8qi2" + [(set (match_operand:V16QI 0 "nonimmediate_operand") + (vec_concat:V16QI + (unspec:V8QI + [(match_operand:V8SI 1 "register_operand")] + UNSPEC_VPMOVSSDB) + (match_dup 2)))] + "TARGET_AVX10V2AUX" + "operands[2] = CONST0_RTX (V8QImode);") + +(define_insn "*avx10v2aux_sym_truncatev8siv8qi2" + [(set (match_operand:V16QI 0 "register_operand" "=v") + (vec_concat:V16QI + (unspec:V8QI + [(match_operand:V8SI 1 "register_operand" "v")] + UNSPEC_VPMOVSSDB) + (match_operand:V8QI 2 "const0_operand")))] + "TARGET_AVX10V2AUX" + "vpmovssdb\t{%1, %0|%0, %1}" + [(set_attr "type" "ssemov") + (set_attr "prefix" "evex") + (set_attr "mode" "OI")]) + +(define_expand "avx10v2aux_sym_truncatev4siv4qi2_mask" + [(set (match_operand:V16QI 0 "nonimmediate_operand") + (vec_concat:V16QI + (vec_merge:V4QI + (unspec:V4QI + [(match_operand:V4SI 1 "register_operand")] + UNSPEC_VPMOVSSDB) + (vec_select:V4QI + (match_operand:V16QI 2 "nonimm_or_0_operand") + (parallel [(const_int 0) (const_int 1) + (const_int 2) (const_int 3)])) + (match_operand:QI 3 "register_operand")) + (match_dup 4)))] + "TARGET_AVX10V2AUX" + "operands[4] = CONST0_RTX (V12QImode);") + +(define_insn "*avx10v2aux_sym_truncatev4siv4qi2_mask" + [(set (match_operand:V16QI 0 "register_operand" "=v") + (vec_concat:V16QI + (vec_merge:V4QI + (unspec:V4QI + [(match_operand:V4SI 1 "register_operand" "v")] + UNSPEC_VPMOVSSDB) + (vec_select:V4QI + (match_operand:V16QI 2 "nonimm_or_0_operand" "0C") + (parallel [(const_int 0) (const_int 1) + (const_int 2) (const_int 3)])) + (match_operand:QI 3 "register_operand" "Yk")) + (match_operand:V12QI 4 "const0_operand")))] + "TARGET_AVX10V2AUX" + "vpmovssdb\t{%1, %0%{%3%}%N2|%0%{%3%}%N2, %1}" + [(set_attr "type" "ssemov") + (set_attr "prefix" "evex") + (set_attr "mode" "TI")]) + +(define_expand "avx10v2aux_sym_truncatev8siv8qi2_mask" + [(set (match_operand:V16QI 0 "nonimmediate_operand") + (vec_concat:V16QI + (vec_merge:V8QI + (unspec:V8QI + [(match_operand:V8SI 1 "register_operand")] + UNSPEC_VPMOVSSDB) + (vec_select:V8QI + (match_operand:V16QI 2 "nonimm_or_0_operand") + (parallel [(const_int 0) (const_int 1) + (const_int 2) (const_int 3) + (const_int 4) (const_int 5) + (const_int 6) (const_int 7)])) + (match_operand:QI 3 "register_operand")) + (match_dup 4)))] + "TARGET_AVX10V2AUX" + "operands[4] = CONST0_RTX (V8QImode);") + +(define_insn "*avx10v2aux_sym_truncatev8siv8qi2_mask" + [(set (match_operand:V16QI 0 "register_operand" "=v") + (vec_concat:V16QI + (vec_merge:V8QI + (unspec:V8QI + [(match_operand:V8SI 1 "register_operand" "v")] + UNSPEC_VPMOVSSDB) + (vec_select:V8QI + (match_operand:V16QI 2 "nonimm_or_0_operand" "0C") + (parallel [(const_int 0) (const_int 1) + (const_int 2) (const_int 3) + (const_int 4) (const_int 5) + (const_int 6) (const_int 7)])) + (match_operand:QI 3 "register_operand" "Yk")) + (match_operand:V8QI 4 "const0_operand")))] + "TARGET_AVX10V2AUX" + "vpmovssdb\t{%1, %0%{%3%}%N2|%0%{%3%}%N2, %1}" + [(set_attr "type" "ssemov") + (set_attr "prefix" "evex") + (set_attr "mode" "OI")]) + +(define_insn "*avx10v2aux_sym_truncatev16siv16qi2" + [(set (match_operand:V16QI 0 "nonimmediate_operand" "=v,m") + (unspec:V16QI + [(match_operand:V16SI 1 "register_operand" "v,v")] + UNSPEC_VPMOVSSDB))] + "TARGET_AVX10V2AUX" + "vpmovssdb\t{%1, %0|%0, %1}" + [(set_attr "type" "ssemov") + (set_attr "memory" "none,store") + (set_attr "prefix" "evex") + (set_attr "mode" "XI")]) + +(define_insn "avx10v2aux_sym_truncatev16siv16qi2_mask" + [(set (match_operand:V16QI 0 "nonimmediate_operand" "=v,m") + (vec_merge:V16QI + (unspec:V16QI + [(match_operand:V16SI 1 "register_operand" "v,v")] + UNSPEC_VPMOVSSDB) + (match_operand:V16QI 2 "nonimm_or_0_operand" "0C,0") + (match_operand:HI 3 "register_operand" "Yk,Yk")))] + "TARGET_AVX10V2AUX" + "vpmovssdb\t{%1, %0%{%3%}%N2|%0%{%3%}%N2, %1}" + [(set_attr "type" "ssemov") + (set_attr "memory" "none,store") + (set_attr "prefix" "evex") + (set_attr "mode" "XI")]) + +(define_expand "avx10v2aux_sym_truncatev16siv16qi2_mask_store" + [(set (match_operand:V16QI 0 "memory_operand") + (vec_merge:V16QI + (unspec:V16QI + [(match_operand:V16SI 1 "register_operand")] + UNSPEC_VPMOVSSDB) + (match_dup 0) + (match_operand:HI 2 "register_operand")))] + "TARGET_AVX10V2AUX") + +(define_insn "*avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_store_1" + [(set (match_operand:<pmov_dst_3> 0 "memory_operand" "=m") + (unspec:<pmov_dst_3> + [(match_operand:VI4_AVX2 1 "register_operand" "v")] + UNSPEC_VPMOVSSDB))] + "TARGET_AVX10V2AUX" + "vpmovssdb\t{%1, %0|%0, %1}" + [(set_attr "type" "ssemov") + (set_attr "memory" "store") + (set_attr "prefix" "evex") + (set_attr "mode" "<sseinsnmode>")]) + +(define_insn_and_split "*avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_store_2" + [(set (match_operand:<pmovss_mem_dest> 0 "memory_operand") + (vec_select:<pmovss_mem_dest> + (subreg:<pmovss_sel_vec> + (vec_concat:V16QI + (unspec:<pmov_dst_3> + [(match_operand:VI4_AVX2 1 "register_operand")] + UNSPEC_VPMOVSSDB) + (match_operand:<pmov_dst_zeroed_3> 2 "const0_operand")) 0) + (parallel [(const_int 0)])))] + "TARGET_AVX10V2AUX && ix86_pre_reload_split ()" + "#" + "&& 1" + [(set (match_dup 0) + (unspec:<pmov_dst_3> [(match_dup 1)] UNSPEC_VPMOVSSDB))] + "operands[0] = adjust_address_nv (operands[0], <pmov_dst_3>mode, 0);") + +(define_insn "avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_mask_store_1" + [(set (match_operand:<pmov_dst_3> 0 "memory_operand" "=m") + (vec_merge:<pmov_dst_3> + (unspec:<pmov_dst_3> + [(match_operand:VI4_AVX2 1 "register_operand" "v")] + UNSPEC_VPMOVSSDB) + (match_dup 0) + (match_operand:<avx512fmaskmode> 2 "register_operand" "Yk")))] + "TARGET_AVX10V2AUX" + "vpmovssdb\t{%1, %0%{%2%}|%0%{%2%}, %1}" + [(set_attr "type" "ssemov") + (set_attr "memory" "store") + (set_attr "prefix" "evex") + (set_attr "mode" "<sseinsnmode>")]) + +(define_expand "avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_mask_store_2" + [(match_operand:<pmov_dst_3> 0 "memory_operand") + (unspec:<pmov_dst_3> + [(match_operand:VI4_AVX2 1 "register_operand")] + UNSPEC_VPMOVSSDB) + (match_operand:<avx512fmaskmode> 2 "register_operand")] + "TARGET_AVX10V2AUX" +{ + operands[0] = adjust_address_nv (operands[0], <pmov_dst_3>mode, 0); + emit_insn (gen_avx10v2aux_sym_truncate<mode>v<ssescalarnum>qi2_mask_store_1 + (operands[0], operands[1], operands[2])); + DONE; +}) diff --git a/gcc/testsuite/g++.dg/other/i386-2.C b/gcc/testsuite/g++.dg/other/i386-2.C index aae565053dc..31775c203b9 100644 --- a/gcc/testsuite/g++.dg/other/i386-2.C +++ b/gcc/testsuite/g++.dg/other/i386-2.C @@ -1,5 +1,5 @@ /* { dg-do compile { target i?86-*-* x86_64-*-* } } */ -/* { dg-options "-O -pedantic-errors -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mavx512vp2intersect -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mcmpccxadd -mamx-fp16 -mprefetchi -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs" } */ +/* { dg-options "-O -pedantic-errors -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mavx512vp2intersect -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mcmpccxadd -mamx-fp16 -mprefetchi -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs -mavx10v2aux" } */ /* { dg-skip-if "requires hosted libstdc++ for cstdlib malloc" { ! hostedlib } } */ /* Test that {,x,e,p,t,s,w,a,b,i}mmintrin.h, mm3dnow.h, fma4intrin.h, @@ -7,7 +7,7 @@ popcntintrin.h, fmaintrin.h, pkuintrin.h, avx512vpopcntdqintrin.h, gfniintrin.h, avx512bitalgintrin.h, avx512vp2intersectintrin.h, tsxldtrkintrin.h, amxtileintrin.h, amxint8intrin.h, amxbf16intrin.h, - avx512vp2intersectvlintrin.h and mm_malloc.h.h are usable + avx512vp2intersectvlintrin.h, avx10v2auxintrin.h and mm_malloc.h.h are usable with -O -pedantic-errors. */ #include <x86intrin.h> diff --git a/gcc/testsuite/g++.dg/other/i386-3.C b/gcc/testsuite/g++.dg/other/i386-3.C index f87910f6b9d..9ee2396a8be 100644 --- a/gcc/testsuite/g++.dg/other/i386-3.C +++ b/gcc/testsuite/g++.dg/other/i386-3.C @@ -1,5 +1,5 @@ /* { dg-do compile { target i?86-*-* x86_64-*-* } } */ -/* { dg-options "-O -fkeep-inline-functions -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mavx512vp2intersect -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mcmpccxadd -mamx-fp16 -mprefetchi -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs" } */ +/* { dg-options "-O -fkeep-inline-functions -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mavx512vp2intersect -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mcmpccxadd -mamx-fp16 -mprefetchi -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs -mavx10v2aux" } */ /* { dg-skip-if "requires hosted libstdc++ for cstdlib malloc" { ! hostedlib } } */ /* Test that {,x,e,p,t,s,w,a,b,i}mmintrin.h, mm3dnow.h, fma4intrin.h, @@ -7,7 +7,7 @@ popcntintrin.h, fmaintrin.h, pkuintrin.h, avx512vpopcntdqintrin.h, gfniintrin.h, avx512bitalgintrin.h, avx512vp2intersectintrin.h, tsxldtrkintrin.h, amxtileintrin.h, amxint8intrin.h, amxbf16intrin.h, - avx512vp2intersectvlintrin.h and mm_malloc.h are usable + avx512vp2intersectvlintrin.h, avx10v2auxintrin.h and mm_malloc.h are usable with -O -fkeep-inline-functions. */ #include <x86intrin.h> diff --git a/gcc/testsuite/gcc.target/i386/avx-1.c b/gcc/testsuite/gcc.target/i386/avx-1.c index 5da06b539f1..eb000759030 100644 --- a/gcc/testsuite/gcc.target/i386/avx-1.c +++ b/gcc/testsuite/gcc.target/i386/avx-1.c @@ -1,5 +1,5 @@ /* { dg-do compile } */ -/* { dg-options "-O2 -Werror-implicit-function-declaration -march=k8 -m3dnow -mavx -mavx2 -maes -mpclmul -mgfni -mprefetchi -mavx10.2 -mmovrs" } */ +/* { dg-options "-O2 -Werror-implicit-function-declaration -march=k8 -m3dnow -mavx -mavx2 -maes -mpclmul -mgfni -mprefetchi -mavx10.2 -mmovrs -mavx10v2aux" } */ /* { dg-add-options bind_pic_locally } */ #include <mm_malloc.h> @@ -913,6 +913,11 @@ #define __builtin_ia32_minmaxsh_mask_round(A, B, C, D, E, F) __builtin_ia32_minmaxsh_mask_round (A, B, 4, D, E, 4) #define __builtin_ia32_minmaxss_mask_round(A, B, C, D, E, F) __builtin_ia32_minmaxss_mask_round (A, B, 4, D, E, 4) +/* avx10v2auxintrin.h */ +#define __builtin_ia32_vunpackb128_mask(A, B, C, D) __builtin_ia32_vunpackb128_mask(A, 8, C, D) +#define __builtin_ia32_vunpackb256_mask(A, B, C, D) __builtin_ia32_vunpackb256_mask(A, 8, C, D) +#define __builtin_ia32_vunpackb512_mask(A, B, C, D) __builtin_ia32_vunpackb512_mask(A, 8, C, D) + #include <wmmintrin.h> #include <immintrin.h> #include <mm3dnow.h> diff --git a/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1i.c b/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1i.c new file mode 100644 index 00000000000..9fe7a163dda --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1i.c @@ -0,0 +1,36 @@ +/* { dg-do compile } */ +/* { dg-options "-mavx10v2aux -O2 -fno-fuse-ops-with-volatile-access" } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\r]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\r]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\r]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\r]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\r]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\r]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ + +#include <immintrin.h> + +volatile __m128i x128i; +volatile __m256i x256i; +volatile __m512i x512i; +volatile __mmask16 m16; +volatile __mmask32 m32; +volatile __mmask64 m64; + +void extern +avx10v2aux_vunpack_test (void) +{ + x128i = _mm_unpack_epi8 (x128i, 8); + x128i = _mm_mask_unpack_epi8 (x128i, m16, x128i, 8); + x128i = _mm_maskz_unpack_epi8 (m16, x128i, 8); + + x256i = _mm256_unpack_epi8 (x256i, 16); + x256i = _mm256_mask_unpack_epi8 (x256i, m32, x256i, 16); + x256i = _mm256_maskz_unpack_epi8 (m32, x256i, 16); + + x512i = _mm512_unpack_epi8 (x512i, 16); + x512i = _mm512_mask_unpack_epi8 (x512i, m64, x512i, 16); + x512i = _mm512_maskz_unpack_epi8 (m64, x512i, 16); +} diff --git a/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1j.c b/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1j.c new file mode 100644 index 00000000000..630968a7803 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1j.c @@ -0,0 +1,43 @@ +/* { dg-do compile } */ +/* { dg-options "-mavx10v2aux -O2 -fno-fuse-ops-with-volatile-access" } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+\[^\n\r]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+%xmm\[0-9\]+, \\(\[^\{\n\]*\\)\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+%ymm\[0-9\]+, \\(\[^\{\n\]*\\)\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vpmovssdb\[ \\t\]+%zmm\[0-9\]+, \\(\[^\{\n\]*\\)\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ + +#include <immintrin.h> + +volatile __m128i x128i; +volatile __m256i x256i; +volatile __m512i x512i; +volatile __m128i res128i; +volatile __mmask8 m8; +volatile __mmask16 m16; +char *p; + +void extern +avx10v2aux_vpmovssdb_test (void) +{ + res128i = _mm_cvtss_epi32_epi8 (x128i); + res128i = _mm_mask_cvtss_epi32_epi8 (res128i, m8, x128i); + res128i = _mm_maskz_cvtss_epi32_epi8 (m8, x128i); + _mm_mask_cvtss_epi32_storeu_epi8 ((void *) p, m8, x128i); + + res128i = _mm256_cvtss_epi32_epi8 (x256i); + res128i = _mm256_mask_cvtss_epi32_epi8 (res128i, m8, x256i); + res128i = _mm256_maskz_cvtss_epi32_epi8 (m8, x256i); + _mm256_mask_cvtss_epi32_storeu_epi8 ((void *) p, m8, x256i); + + res128i = _mm512_cvtss_epi32_epi8 (x512i); + res128i = _mm512_mask_cvtss_epi32_epi8 (res128i, m16, x512i); + res128i = _mm512_maskz_cvtss_epi32_epi8 (m16, x512i); + _mm512_mask_cvtss_epi32_storeu_epi8 ((void *) p, m16, x512i); +} diff --git a/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1k.c b/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1k.c new file mode 100644 index 00000000000..49cef60fc58 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1k.c @@ -0,0 +1,29 @@ +/* Exercise the non-__OPTIMIZE__ (macro) path of the vunpackb intrinsics. */ +/* { dg-do compile } */ +/* { dg-options "-mavx10v2aux -O0" } */ +/* { dg-final { scan-assembler-times "vunpackb\[ \\t\]" 9 } } */ + +#include <immintrin.h> + +volatile __m128i x128i; +volatile __m256i x256i; +volatile __m512i x512i; +volatile __mmask16 m16; +volatile __mmask32 m32; +volatile __mmask64 m64; + +void extern +avx10v2aux_vunpack_noopt_test (void) +{ + x128i = _mm_unpack_epi8 (x128i, 8); + x128i = _mm_mask_unpack_epi8 (x128i, m16, x128i, 9); + x128i = _mm_maskz_unpack_epi8 (m16, x128i, 10); + + x256i = _mm256_unpack_epi8 (x256i, 16); + x256i = _mm256_mask_unpack_epi8 (x256i, m32, x256i, 17); + x256i = _mm256_maskz_unpack_epi8 (m32, x256i, 40); + + x512i = _mm512_unpack_epi8 (x512i, 45); + x512i = _mm512_mask_unpack_epi8 (x512i, m64, x512i, 48); + x512i = _mm512_maskz_unpack_epi8 (m64, x512i, 60); +} diff --git a/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1l.c b/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1l.c new file mode 100644 index 00000000000..3893e5e0529 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/avx10v2aux-convert-1l.c @@ -0,0 +1,27 @@ +/* { dg-do compile } */ +/* { dg-options "-mavx10v2aux -O0" } */ + +#include <immintrin.h> + +volatile __m128i x128i; +volatile __m256i x256i; +volatile __m512i x512i; +volatile __mmask16 m16; +volatile __mmask32 m32; +volatile __mmask64 m64; + +void extern +avx10v2aux_vunpack_imm_range_test (void) +{ + x128i = _mm_unpack_epi8 (x128i, 1); /* { dg-error "the last argument must not use reserved value immediate" } */ + x128i = _mm_mask_unpack_epi8 (x128i, m16, x128i, 14); /* { dg-error "the last argument must not use reserved value immediate" } */ + x128i = _mm_maskz_unpack_epi8 (m16, x128i, 21); /* { dg-error "the last argument must not use reserved value immediate" } */ + + x256i = _mm256_unpack_epi8 (x256i, 22); /* { dg-error "the last argument must not use reserved value immediate" } */ + x256i = _mm256_mask_unpack_epi8 (x256i, m32, x256i, 25); /* { dg-error "the last argument must not use reserved value immediate" } */ + x256i = _mm256_maskz_unpack_epi8 (m32, x256i, 29); /* { dg-error "the last argument must not use reserved value immediate" } */ + + x512i = _mm512_unpack_epi8 (x512i, 30); /* { dg-error "the last argument must not use reserved value immediate" } */ + x512i = _mm512_mask_unpack_epi8 (x512i, m64, x512i, 31); /* { dg-error "the last argument must not use reserved value immediate" } */ + x512i = _mm512_maskz_unpack_epi8 (m64, x512i, 50); /* { dg-error "the last argument must not use reserved value immediate" } */ +} diff --git a/gcc/testsuite/gcc.target/i386/funcspec-56.inc b/gcc/testsuite/gcc.target/i386/funcspec-56.inc index 87e38a562e0..241c36e8cfd 100644 --- a/gcc/testsuite/gcc.target/i386/funcspec-56.inc +++ b/gcc/testsuite/gcc.target/i386/funcspec-56.inc @@ -92,6 +92,7 @@ extern void test_amx_avx512 (void) __attribute__((__target__("amx-avx512"))); extern void test_amx_fp8 (void) __attribute__((__target__("amx-fp8"))); extern void test_movrs (void) __attribute__((__target__("movrs"))); extern void test_amx_movrs (void) __attribute__((__target__("amx-movrs"))); +extern void test_avx10v2aux (void) __attribute__((__target__("avx10v2aux"))); extern void test_no_sgx (void) __attribute__((__target__("no-sgx"))); extern void test_no_avx512vpopcntdq(void) __attribute__((__target__("no-avx512vpopcntdq"))); @@ -185,6 +186,7 @@ extern void test_no_amx_avx512 (void) __attribute__((__target__("no-amx-avx512" extern void test_no_amx_fp8 (void) __attribute__((__target__("no-amx-fp8"))); extern void test_no_movrs (void) __attribute__((__target__("no-movrs"))); extern void test_no_amx_movrs (void) __attribute__((__target__("no-amx-movrs"))); +extern void test_no_avx10v2aux (void) __attribute__((__target__("no-avx10v2aux"))); extern void test_arch_nocona (void) __attribute__((__target__("arch=nocona"))); extern void test_arch_core2 (void) __attribute__((__target__("arch=core2"))); diff --git a/gcc/testsuite/gcc.target/i386/sse-12.c b/gcc/testsuite/gcc.target/i386/sse-12.c index e1c70fc41fd..6b05962b3c2 100644 --- a/gcc/testsuite/gcc.target/i386/sse-12.c +++ b/gcc/testsuite/gcc.target/i386/sse-12.c @@ -3,7 +3,7 @@ popcntintrin.h gfniintrin.h and mm_malloc.h are usable with -O -std=c89 -pedantic-errors. */ /* { dg-do compile } */ -/* { dg-options "-O -std=c89 -pedantic-errors -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mavx512vp2intersect -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mamx-fp16 -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs" } */ +/* { dg-options "-O -std=c89 -pedantic-errors -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mavx512vp2intersect -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mamx-fp16 -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs -mavx10v2aux" } */ #include <x86intrin.h> diff --git a/gcc/testsuite/gcc.target/i386/sse-13.c b/gcc/testsuite/gcc.target/i386/sse-13.c index 2835886f4f2..a062aa90355 100644 --- a/gcc/testsuite/gcc.target/i386/sse-13.c +++ b/gcc/testsuite/gcc.target/i386/sse-13.c @@ -1,5 +1,5 @@ /* { dg-do compile } */ -/* { dg-options "-O2 -Werror-implicit-function-declaration -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mavx512vp2intersect -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mcmpccxadd -mamx-fp16 -mprefetchi -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs" } */ +/* { dg-options "-O2 -Werror-implicit-function-declaration -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mavx512vp2intersect -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mcmpccxadd -mamx-fp16 -mprefetchi -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs -mavx10v2aux" } */ /* { dg-add-options bind_pic_locally } */ #include <mm_malloc.h> @@ -920,4 +920,9 @@ #define __builtin_ia32_minmaxsh_mask_round(A, B, C, D, E, F) __builtin_ia32_minmaxsh_mask_round (A, B, 4, D, E, 4) #define __builtin_ia32_minmaxss_mask_round(A, B, C, D, E, F) __builtin_ia32_minmaxss_mask_round (A, B, 4, D, E, 4) +/* avx10v2auxintrin.h */ +#define __builtin_ia32_vunpackb128_mask(A, B, C, D) __builtin_ia32_vunpackb128_mask(A, 8, C, D) +#define __builtin_ia32_vunpackb256_mask(A, B, C, D) __builtin_ia32_vunpackb256_mask(A, 8, C, D) +#define __builtin_ia32_vunpackb512_mask(A, B, C, D) __builtin_ia32_vunpackb512_mask(A, 8, C, D) + #include <x86intrin.h> diff --git a/gcc/testsuite/gcc.target/i386/sse-14.c b/gcc/testsuite/gcc.target/i386/sse-14.c index 84be5f939a9..67a02604da9 100644 --- a/gcc/testsuite/gcc.target/i386/sse-14.c +++ b/gcc/testsuite/gcc.target/i386/sse-14.c @@ -1,5 +1,5 @@ /* { dg-do compile } */ -/* { dg-options "-O0 -Werror-implicit-function-declaration -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mavx512vp2intersect -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mamx-fp16 -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs" } */ +/* { dg-options "-O0 -Werror-implicit-function-declaration -march=k8 -msse4a -m3dnow -mavx -mavx2 -mfma4 -mxop -maes -mpclmul -mpopcnt -mabm -mlzcnt -mbmi -mbmi2 -mtbm -mlwp -mfsgsbase -mrdrnd -mf16c -mfma -mrtm -mrdseed -mprfchw -madx -mfxsr -mxsaveopt -msha -mxsavec -mxsaves -mclflushopt -mclwb -mmwaitx -mclzero -mpku -msgx -mrdpid -mgfni -mpconfig -mwbnoinvd -menqcmd -mavx512vp2intersect -mserialize -mtsxldtrk -mamx-tile -mamx-int8 -mamx-bf16 -mkl -mwidekl -mavxvnni -mavxifma -mavxvnniint8 -mavxneconvert -mamx-fp16 -mraoint -mamx-complex -mavxvnniint16 -msm3 -msha512 -msm4 -mavx10.2 -mamx-avx512 -mamx-fp8 -mmovrs -mamx-movrs -mavx10v2aux" } */ /* { dg-add-options bind_pic_locally } */ #include <mm_malloc.h> @@ -1192,3 +1192,14 @@ test_4x (_mm_mask_minmax_round_ss, __m128, __m128, __mmask8, __m128, __m128, 100 test_2x (_mm_minmax_round_sh, __m128h, __m128h, __m128h, 100, 4) test_3x (_mm_maskz_minmax_round_sh, __m128h, __mmask8, __m128h, __m128h, 100, 4) test_4x (_mm_mask_minmax_round_sh, __m128h, __m128h, __mmask8, __m128h, __m128h, 100, 4) + +/* avx10v2auxintrin.h */ +test_1(_mm_unpack_epi8, __m128i, __m128i, 10) +test_3(_mm_mask_unpack_epi8, __m128i, __m128i, __mmask16, __m128i, 10) +test_2(_mm_maskz_unpack_epi8, __m128i, __mmask16, __m128i, 10) +test_1(_mm256_unpack_epi8, __m256i, __m256i, 10) +test_3(_mm256_mask_unpack_epi8, __m256i, __m256i, __mmask32, __m256i, 10) +test_2(_mm256_maskz_unpack_epi8, __m256i, __mmask32, __m256i, 10) +test_1(_mm512_unpack_epi8, __m512i, __m512i, 10) +test_3(_mm512_mask_unpack_epi8, __m512i, __m512i, __mmask64, __m512i, 10) +test_2(_mm512_maskz_unpack_epi8, __m512i, __mmask64, __m512i, 10) diff --git a/gcc/testsuite/gcc.target/i386/sse-22.c b/gcc/testsuite/gcc.target/i386/sse-22.c index dd725c0871a..d903d2b9315 100644 --- a/gcc/testsuite/gcc.target/i386/sse-22.c +++ b/gcc/testsuite/gcc.target/i386/sse-22.c @@ -12,7 +12,7 @@ avx5124fmapsintrin.h, avx5124vnniwintrin.h, avx512vpopcntdqintrin.h, avx512bitalgintrin.h, avx512vp2intersectintrin.h, amxtileintrin.h, amxint8intrin.h, amxbf16intrin.h, - avx512vp2intersectvlintrin.h and mm_malloc.h that reference the proper + avx512vp2intersectvlintrin.h, avx10v2auxintrin.h and mm_malloc.h that reference the proper builtin functions. Defining away "extern" and "__inline" results in all of them being compiled as proper functions. */ @@ -103,7 +103,7 @@ #ifndef DIFFERENT_PRAGMAS -#pragma GCC target ("sse4a,3dnow,avx,avx2,fma4,xop,aes,pclmul,popcnt,abm,lzcnt,bmi,bmi2,tbm,lwp,fsgsbase,rdrnd,f16c,rtm,rdseed,prfchw,adx,fxsr,xsaveopt,sha,gfni,avx512vp2intersect,serialize,tsxldtrk,amx-tile,amx-int8,amx-bf16,kl,widekl,avxvnni,avxifma,avxvnniint8,avxneconvert,amx-fp16,raoint,amx-complex,avxvnniint16,sm3,sha512,sm4,avx10.2,amx-avx512,amx-fp8,movrs,amx-movrs") +#pragma GCC target ("sse4a,3dnow,avx,avx2,fma4,xop,aes,pclmul,popcnt,abm,lzcnt,bmi,bmi2,tbm,lwp,fsgsbase,rdrnd,f16c,rtm,rdseed,prfchw,adx,fxsr,xsaveopt,sha,gfni,avx512vp2intersect,serialize,tsxldtrk,amx-tile,amx-int8,amx-bf16,kl,widekl,avxvnni,avxifma,avxvnniint8,avxneconvert,amx-fp16,raoint,amx-complex,avxvnniint16,sm3,sha512,sm4,avx10.2,amx-avx512,amx-fp8,movrs,amx-movrs,avx10v2aux") #endif /* Following intrinsics require immediate arguments. They @@ -220,7 +220,7 @@ test_4 (_mm_cmpestrz, int, __m128i, int, __m128i, int, 1) /* immintrin.h (AVX/AVX2/RDRND/FSGSBASE/F16C/RTM/AVX512F/SHA) */ #ifdef DIFFERENT_PRAGMAS -#pragma GCC target ("avx,avx2,rdrnd,fsgsbase,f16c,rtm,sha,gfni,avx512vp2intersect,serialize,tsxldtrk,amx-tile,amx-int8,amx-bf16,kl,widekl,avxvnni,avxifma,avxvnniint8,avxneconvert,amx-fp16,raoint,amx-complex,avxvnniint16,sm3,sha512,sm4,avx10.2,amx-avx512,amx-fp8,movrs,amx-movrs") +#pragma GCC target ("avx,avx2,rdrnd,fsgsbase,f16c,rtm,sha,gfni,avx512vp2intersect,serialize,tsxldtrk,amx-tile,amx-int8,amx-bf16,kl,widekl,avxvnni,avxifma,avxvnniint8,avxneconvert,amx-fp16,raoint,amx-complex,avxvnniint16,sm3,sha512,sm4,avx10.2,amx-avx512,amx-fp8,movrs,amx-movrs,avx10v2aux") #endif #include <immintrin.h> test_1 (_cvtss_sh, unsigned short, float, 1) @@ -1233,3 +1233,14 @@ test_4x (_mm_mask_minmax_round_ss, __m128, __m128, __mmask8, __m128, __m128, 100 test_2x (_mm_minmax_round_sh, __m128h, __m128h, __m128h, 100, 4) test_3x (_mm_maskz_minmax_round_sh, __m128h, __mmask8, __m128h, __m128h, 100, 4) test_4x (_mm_mask_minmax_round_sh, __m128h, __m128h, __mmask8, __m128h, __m128h, 100, 4) + +/* avx10v2auxintrin.h */ +test_1(_mm_unpack_epi8, __m128i, __m128i, 10) +test_3(_mm_mask_unpack_epi8, __m128i, __m128i, __mmask16, __m128i, 10) +test_2(_mm_maskz_unpack_epi8, __m128i, __mmask16, __m128i, 10) +test_1(_mm256_unpack_epi8, __m256i, __m256i, 10) +test_3(_mm256_mask_unpack_epi8, __m256i, __m256i, __mmask32, __m256i, 10) +test_2(_mm256_maskz_unpack_epi8, __m256i, __mmask32, __m256i, 10) +test_1(_mm512_unpack_epi8, __m512i, __m512i, 10) +test_3(_mm512_mask_unpack_epi8, __m512i, __m512i, __mmask64, __m512i, 10) +test_2(_mm512_maskz_unpack_epi8, __m512i, __mmask64, __m512i, 10) diff --git a/gcc/testsuite/gcc.target/i386/sse-23.c b/gcc/testsuite/gcc.target/i386/sse-23.c index 0a003ca1e91..0258ada227a 100644 --- a/gcc/testsuite/gcc.target/i386/sse-23.c +++ b/gcc/testsuite/gcc.target/i386/sse-23.c @@ -11,7 +11,7 @@ avx5124fmapsintrin.h, avx5124vnniwintrin.h, avx512vpopcntdqintrin.h, avx512bitalgintrin.h, avx512vp2intersectintrin.h, amxtileintrin.h, amxint8intrin.h, amxbf16intrin.h, - avx512vp2intersectvlintrin.h and mm_malloc.h that reference the proper + avx512vp2intersectvlintrin.h, avx10v2auxintrin.h and mm_malloc.h that reference the proper builtin functions. Defining away "extern" and "__inline" results in all of them being compiled as proper functions. */ @@ -895,6 +895,11 @@ #define __builtin_ia32_minmaxsh_mask_round(A, B, C, D, E, F) __builtin_ia32_minmaxsh_mask_round (A, B, 100, D, E, 4) #define __builtin_ia32_minmaxss_mask_round(A, B, C, D, E, F) __builtin_ia32_minmaxss_mask_round (A, B, 100, D, E, 4) -#pragma GCC target ("sse4a,3dnow,avx,avx2,fma4,xop,aes,pclmul,popcnt,abm,lzcnt,bmi,bmi2,tbm,lwp,fsgsbase,rdrnd,f16c,fma,rtm,rdseed,prfchw,adx,fxsr,xsaveopt,sha,xsavec,xsaves,clflushopt,clwb,mwaitx,clzero,pku,sgx,rdpid,gfni,vpclmulqdq,pconfig,wbnoinvd,enqcmd,avx512vp2intersect,serialize,tsxldtrk,amx-tile,amx-int8,amx-bf16,kl,widekl,avxvnni,avxifma,avxvnniint8,avxneconvert,cmpccxadd,amx-fp16,prefetchi,raoint,amx-complex,avxvnniint16,sm3,sha512,sm4,avx10.2,amx-avx512,amx-fp8,movrs,amx-movrs") +/* avx10v2auxintrin.h */ +#define __builtin_ia32_vunpackb128_mask(A, B, C, D) __builtin_ia32_vunpackb128_mask(A, 8, C, D) +#define __builtin_ia32_vunpackb256_mask(A, B, C, D) __builtin_ia32_vunpackb256_mask(A, 8, C, D) +#define __builtin_ia32_vunpackb512_mask(A, B, C, D) __builtin_ia32_vunpackb512_mask(A, 8, C, D) + +#pragma GCC target ("sse4a,3dnow,avx,avx2,fma4,xop,aes,pclmul,popcnt,abm,lzcnt,bmi,bmi2,tbm,lwp,fsgsbase,rdrnd,f16c,fma,rtm,rdseed,prfchw,adx,fxsr,xsaveopt,sha,xsavec,xsaves,clflushopt,clwb,mwaitx,clzero,pku,sgx,rdpid,gfni,vpclmulqdq,pconfig,wbnoinvd,enqcmd,avx512vp2intersect,serialize,tsxldtrk,amx-tile,amx-int8,amx-bf16,kl,widekl,avxvnni,avxifma,avxvnniint8,avxneconvert,cmpccxadd,amx-fp16,prefetchi,raoint,amx-complex,avxvnniint16,sm3,sha512,sm4,avx10.2,amx-avx512,amx-fp8,movrs,amx-movrs,avx10v2aux") #include <x86intrin.h> diff --git a/gcc/testsuite/lib/target-supports.exp b/gcc/testsuite/lib/target-supports.exp index eb2444204a0..bdb84971535 100644 --- a/gcc/testsuite/lib/target-supports.exp +++ b/gcc/testsuite/lib/target-supports.exp @@ -11701,6 +11701,9 @@ proc check_effective_target_avx10v2aux { } { foo () { __asm__ volatile ("vcvtps2bf8\t{%%xmm1, %%xmm0|%%xmm0, %%xmm1}"); + __asm__ volatile ("vcvtbf82ps\t{%%xmm1, %%xmm0|%%xmm0, %%xmm1}"); + __asm__ volatile ("vunpackb\t$1, %%ymm1, %%ymm0"); + __asm__ volatile ("vpmovssdb\t{%%zmm1, %%xmm0|%%xmm0, %%zmm1}"); } } "-mavx10v2aux" ] } -- 2.34.1