gcc/ChangeLog: PR target/118270 * config/i386/avx10_2-512convertintrin.h: Change intrin and builtin name according to new mnemonics. * config/i386/avx10_2convertintrin.h: Ditto. * config/i386/i386-builtin.def (BDESC): Ditto. * config/i386/sse.md (UNSPEC_VCVT2PH2BF8): Rename from UNSPEC_VCVTNE2PH2BF8. (UNSPEC_VCVT2PH2BF8S): Rename from UNSPEC_VCVTNE2PH2BF8S. (UNSPEC_VCVT2PH2HF8): Rename from UNSPEC_VCVTNE2PH2HF8. (UNSPEC_VCVT2PH2HF8S): Rename from UNSPEC_VCVTNE2PH2HF8S. (UNSPEC_CONVERTFP8_PACK): Rename from UNSPEC_NECONVERTFP8_PACK. Adjust UNSPEC name. (convertfp8_pack): Rename from neconvertfp8_pack. Adjust iterator map. (vcvt<neconvertfp8_pack><mode><mask_name>): Rename to... (vcvt<convertfp8_pack><mode><mask_name>): ...this.
gcc/testsuite/ChangeLog: PR target/118270 * gcc.target/i386/avx10_2-512-convert-1.c: Adjust output and intrin call. * gcc.target/i386/avx10_2-512-vcvtne2ph2bf8-2.c: Move to... * gcc.target/i386/avx10_2-512-vcvt2ph2bf8-2.c: ...here. Adjust intrin call. * gcc.target/i386/avx10_2-512-vcvtne2ph2bf8s-2.c: Move to... * gcc.target/i386/avx10_2-512-vcvt2ph2bf8s-2.c: ...here. Adjust intrin call. * gcc.target/i386/avx10_2-512-vcvtne2ph2hf8-2.c: Move to... * gcc.target/i386/avx10_2-512-vcvt2ph2hf8-2.c: ...here. Adjust intrin call. * gcc.target/i386/avx10_2-512-vcvtne2ph2hf8s-2.c: Move to... * gcc.target/i386/avx10_2-512-vcvt2ph2hf8s-2.c: ...here. Adjust intrin call. * gcc.target/i386/avx10_2-convert-1.c: Adjust output and intrin call. * gcc.target/i386/avx10_2-vcvtne2ph2bf8-2.c: Move to... * gcc.target/i386/avx10_2-vcvt2ph2bf8-2.c: ...here. Adjust intrin call. * gcc.target/i386/avx10_2-vcvtne2ph2hf8-2.c: Move to... * gcc.target/i386/avx10_2-vcvt2ph2bf8s-2.c: ...here. Adjust intrin call. * gcc.target/i386/avx10_2-vcvtne2ph2bf8s-2.c: Move to... * gcc.target/i386/avx10_2-vcvt2ph2hf8-2.c: ...here. Adjust intrin call. * gcc.target/i386/avx10_2-vcvtne2ph2hf8s-2.c: Move to... * gcc.target/i386/avx10_2-vcvt2ph2hf8s-2.c: ...here. Adjust intrin call. --- gcc/config/i386/avx10_2-512convertintrin.h | 142 ++++----- gcc/config/i386/avx10_2convertintrin.h | 286 +++++++++--------- gcc/config/i386/i386-builtin.def | 24 +- gcc/config/i386/sse.md | 30 +- .../gcc.target/i386/avx10_2-512-convert-1.c | 56 ++-- ...ph2bf8-2.c => avx10_2-512-vcvt2ph2bf8-2.c} | 6 +- ...2bf8s-2.c => avx10_2-512-vcvt2ph2bf8s-2.c} | 6 +- ...ph2hf8-2.c => avx10_2-512-vcvt2ph2hf8-2.c} | 6 +- ...2hf8s-2.c => avx10_2-512-vcvt2ph2hf8s-2.c} | 6 +- .../gcc.target/i386/avx10_2-convert-1.c | 104 +++---- ...tne2ph2bf8-2.c => avx10_2-vcvt2ph2bf8-2.c} | 4 +- ...ne2ph2hf8-2.c => avx10_2-vcvt2ph2bf8s-2.c} | 4 +- ...ne2ph2bf8s-2.c => avx10_2-vcvt2ph2hf8-2.c} | 4 +- ...e2ph2hf8s-2.c => avx10_2-vcvt2ph2hf8s-2.c} | 4 +- 14 files changed, 341 insertions(+), 341 deletions(-) rename gcc/testsuite/gcc.target/i386/{avx10_2-512-vcvtne2ph2bf8-2.c => avx10_2-512-vcvt2ph2bf8-2.c} (89%) rename gcc/testsuite/gcc.target/i386/{avx10_2-512-vcvtne2ph2bf8s-2.c => avx10_2-512-vcvt2ph2bf8s-2.c} (89%) rename gcc/testsuite/gcc.target/i386/{avx10_2-512-vcvtne2ph2hf8-2.c => avx10_2-512-vcvt2ph2hf8-2.c} (89%) rename gcc/testsuite/gcc.target/i386/{avx10_2-512-vcvtne2ph2hf8s-2.c => avx10_2-512-vcvt2ph2hf8s-2.c} (89%) rename gcc/testsuite/gcc.target/i386/{avx10_2-vcvtne2ph2bf8-2.c => avx10_2-vcvt2ph2bf8-2.c} (78%) rename gcc/testsuite/gcc.target/i386/{avx10_2-vcvtne2ph2hf8-2.c => avx10_2-vcvt2ph2bf8s-2.c} (78%) rename gcc/testsuite/gcc.target/i386/{avx10_2-vcvtne2ph2bf8s-2.c => avx10_2-vcvt2ph2hf8-2.c} (78%) rename gcc/testsuite/gcc.target/i386/{avx10_2-vcvtne2ph2hf8s-2.c => avx10_2-vcvt2ph2hf8s-2.c} (78%) diff --git a/gcc/config/i386/avx10_2-512convertintrin.h b/gcc/config/i386/avx10_2-512convertintrin.h index 23b2636139d..c753dd7a946 100644 --- a/gcc/config/i386/avx10_2-512convertintrin.h +++ b/gcc/config/i386/avx10_2-512convertintrin.h @@ -265,134 +265,134 @@ _mm512_maskz_cvtbiassph_phf8 (__mmask32 __U, __m512i __A, __m512h __B) extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_cvtne2ph_pbf8 (__m512h __A, __m512h __B) +_mm512_cvt2ph_bf8 (__m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2bf8512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) - _mm512_setzero_si512 (), - (__mmask64) -1); + return (__m512i) __builtin_ia32_vcvt2ph2bf8512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) -1); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_mask_cvtne2ph_pbf8 (__m512i __W, __mmask64 __U, - __m512h __A, __m512h __B) +_mm512_mask_cvt2ph_bf8 (__m512i __W, __mmask64 __U, + __m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2bf8512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) __W, - (__mmask64) __U); + return (__m512i) __builtin_ia32_vcvt2ph2bf8512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) __W, + (__mmask64) __U); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_maskz_cvtne2ph_pbf8 (__mmask64 __U, __m512h __A, __m512h __B) +_mm512_maskz_cvt2ph_bf8 (__mmask64 __U, __m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2bf8512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) - _mm512_setzero_si512 (), - (__mmask64) __U); + return (__m512i) __builtin_ia32_vcvt2ph2bf8512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) __U); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_cvtnes2ph_pbf8 (__m512h __A, __m512h __B) +_mm512_cvts2ph_bf8 (__m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2bf8s512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) - _mm512_setzero_si512 (), - (__mmask64) -1); + return (__m512i) __builtin_ia32_vcvt2ph2bf8s512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) -1); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_mask_cvtnes2ph_pbf8 (__m512i __W, __mmask64 __U, - __m512h __A, __m512h __B) +_mm512_mask_cvts2ph_bf8 (__m512i __W, __mmask64 __U, + __m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2bf8s512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) __W, - (__mmask64) __U); + return (__m512i) __builtin_ia32_vcvt2ph2bf8s512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) __W, + (__mmask64) __U); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_maskz_cvtnes2ph_pbf8 (__mmask64 __U, __m512h __A, __m512h __B) +_mm512_maskz_cvts2ph_bf8 (__mmask64 __U, __m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2bf8s512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) - _mm512_setzero_si512 (), - (__mmask64) __U); + return (__m512i) __builtin_ia32_vcvt2ph2bf8s512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) __U); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_cvtne2ph_phf8 (__m512h __A, __m512h __B) +_mm512_cvt2ph_hf8 (__m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2hf8512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) - _mm512_setzero_si512 (), - (__mmask64) -1); + return (__m512i) __builtin_ia32_vcvt2ph2hf8512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) -1); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_mask_cvtne2ph_phf8 (__m512i __W, __mmask64 __U, - __m512h __A, __m512h __B) +_mm512_mask_cvt2ph_hf8 (__m512i __W, __mmask64 __U, + __m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2hf8512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) __W, - (__mmask64) __U); + return (__m512i) __builtin_ia32_vcvt2ph2hf8512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) __W, + (__mmask64) __U); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_maskz_cvtne2ph_phf8 (__mmask64 __U, __m512h __A, __m512h __B) +_mm512_maskz_cvt2ph_hf8 (__mmask64 __U, __m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2hf8512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) - _mm512_setzero_si512 (), - (__mmask64) __U); + return (__m512i) __builtin_ia32_vcvt2ph2hf8512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) __U); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_cvtnes2ph_phf8 (__m512h __A, __m512h __B) +_mm512_cvts2ph_hf8 (__m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2hf8s512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) - _mm512_setzero_si512 (), - (__mmask64) -1); + return (__m512i) __builtin_ia32_vcvt2ph2hf8s512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) -1); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_mask_cvtnes2ph_phf8 (__m512i __W, __mmask64 __U, +_mm512_mask_cvts2ph_hf8 (__m512i __W, __mmask64 __U, __m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2hf8s512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) __W, - (__mmask64) __U); + return (__m512i) __builtin_ia32_vcvt2ph2hf8s512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) __W, + (__mmask64) __U); } extern __inline__ __m512i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm512_maskz_cvtnes2ph_phf8 (__mmask64 __U, __m512h __A, __m512h __B) +_mm512_maskz_cvts2ph_hf8 (__mmask64 __U, __m512h __A, __m512h __B) { - return (__m512i) __builtin_ia32_vcvtne2ph2hf8s512_mask ((__v32hf) __A, - (__v32hf) __B, - (__v64qi) - _mm512_setzero_si512 (), - (__mmask64) __U); + return (__m512i) __builtin_ia32_vcvt2ph2hf8s512_mask ((__v32hf) __A, + (__v32hf) __B, + (__v64qi) + _mm512_setzero_si512 (), + (__mmask64) __U); } extern __inline__ __m512h diff --git a/gcc/config/i386/avx10_2convertintrin.h b/gcc/config/i386/avx10_2convertintrin.h index 4b8a9e14011..45d2bff3c96 100644 --- a/gcc/config/i386/avx10_2convertintrin.h +++ b/gcc/config/i386/avx10_2convertintrin.h @@ -418,266 +418,266 @@ _mm256_maskz_cvtbiassph_phf8 (__mmask16 __U, __m256i __A, __m256h __B) extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_cvtne2ph_pbf8 (__m128h __A, __m128h __B) +_mm_cvt2ph_bf8 (__m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2bf8128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) - _mm_setzero_si128 (), - (__mmask16) -1); + return (__m128i) __builtin_ia32_vcvt2ph2bf8128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) -1); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_mask_cvtne2ph_pbf8 (__m128i __W, __mmask16 __U, - __m128h __A, __m128h __B) +_mm_mask_cvt2ph_bf8 (__m128i __W, __mmask16 __U, + __m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2bf8128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) __W, - (__mmask16) __U); + return (__m128i) __builtin_ia32_vcvt2ph2bf8128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) __W, + (__mmask16) __U); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_maskz_cvtne2ph_pbf8 (__mmask16 __U, __m128h __A, __m128h __B) +_mm_maskz_cvt2ph_bf8 (__mmask16 __U, __m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2bf8128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) - _mm_setzero_si128 (), - (__mmask16) __U); + return (__m128i) __builtin_ia32_vcvt2ph2bf8128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) __U); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_cvtne2ph_pbf8 (__m256h __A, __m256h __B) +_mm256_cvt2ph_bf8 (__m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2bf8256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) - _mm256_setzero_si256 (), - (__mmask32) -1); + return (__m256i) __builtin_ia32_vcvt2ph2bf8256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) -1); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_mask_cvtne2ph_pbf8 (__m256i __W, __mmask32 __U, - __m256h __A, __m256h __B) +_mm256_mask_cvt2ph_bf8 (__m256i __W, __mmask32 __U, + __m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2bf8256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) __W, - (__mmask32) __U); + return (__m256i) __builtin_ia32_vcvt2ph2bf8256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) __W, + (__mmask32) __U); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_maskz_cvtne2ph_pbf8 (__mmask32 __U, __m256h __A, __m256h __B) +_mm256_maskz_cvt2ph_bf8 (__mmask32 __U, __m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2bf8256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) - _mm256_setzero_si256 (), - (__mmask32) __U); + return (__m256i) __builtin_ia32_vcvt2ph2bf8256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) __U); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_cvtnes2ph_pbf8 (__m128h __A, __m128h __B) +_mm_cvts2ph_bf8 (__m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2bf8s128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) - _mm_setzero_si128 (), - (__mmask16) -1); + return (__m128i) __builtin_ia32_vcvt2ph2bf8s128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) -1); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_mask_cvtnes2ph_pbf8 (__m128i __W, __mmask16 __U, - __m128h __A, __m128h __B) +_mm_mask_cvts2ph_bf8 (__m128i __W, __mmask16 __U, + __m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2bf8s128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) __W, - (__mmask16) __U); + return (__m128i) __builtin_ia32_vcvt2ph2bf8s128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) __W, + (__mmask16) __U); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_maskz_cvtnes2ph_pbf8 (__mmask16 __U, __m128h __A, __m128h __B) +_mm_maskz_cvts2ph_bf8 (__mmask16 __U, __m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2bf8s128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) - _mm_setzero_si128 (), - (__mmask16) __U); + return (__m128i) __builtin_ia32_vcvt2ph2bf8s128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) __U); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_cvtnes2ph_pbf8 (__m256h __A, __m256h __B) +_mm256_cvts2ph_bf8 (__m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2bf8s256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) - _mm256_setzero_si256 (), - (__mmask32) -1); + return (__m256i) __builtin_ia32_vcvt2ph2bf8s256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) -1); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_mask_cvtnes2ph_pbf8 (__m256i __W, __mmask32 __U, +_mm256_mask_cvts2ph_bf8 (__m256i __W, __mmask32 __U, __m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2bf8s256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) __W, - (__mmask32) __U); + return (__m256i) __builtin_ia32_vcvt2ph2bf8s256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) __W, + (__mmask32) __U); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_maskz_cvtnes2ph_pbf8 (__mmask32 __U, __m256h __A, __m256h __B) +_mm256_maskz_cvts2ph_bf8 (__mmask32 __U, __m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2bf8s256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) - _mm256_setzero_si256 (), - (__mmask32) __U); + return (__m256i) __builtin_ia32_vcvt2ph2bf8s256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) __U); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_cvtne2ph_phf8 (__m128h __A, __m128h __B) +_mm_cvt2ph_hf8 (__m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2hf8128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) - _mm_setzero_si128 (), - (__mmask16) -1); + return (__m128i) __builtin_ia32_vcvt2ph2hf8128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) -1); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_mask_cvtne2ph_phf8 (__m128i __W, __mmask16 __U, - __m128h __A, __m128h __B) +_mm_mask_cvt2ph_hf8 (__m128i __W, __mmask16 __U, + __m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2hf8128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) __W, - (__mmask16) __U); + return (__m128i) __builtin_ia32_vcvt2ph2hf8128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) __W, + (__mmask16) __U); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_maskz_cvtne2ph_phf8 (__mmask16 __U, __m128h __A, __m128h __B) +_mm_maskz_cvt2ph_hf8 (__mmask16 __U, __m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2hf8128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) - _mm_setzero_si128 (), - (__mmask16) __U); + return (__m128i) __builtin_ia32_vcvt2ph2hf8128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) __U); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_cvtne2ph_phf8 (__m256h __A, __m256h __B) +_mm256_cvt2ph_hf8 (__m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2hf8256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) - _mm256_setzero_si256 (), - (__mmask32) -1); + return (__m256i) __builtin_ia32_vcvt2ph2hf8256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) -1); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_mask_cvtne2ph_phf8 (__m256i __W, __mmask32 __U, - __m256h __A, __m256h __B) +_mm256_mask_cvt2ph_hf8 (__m256i __W, __mmask32 __U, + __m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2hf8256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) __W, - (__mmask32) __U); + return (__m256i) __builtin_ia32_vcvt2ph2hf8256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) __W, + (__mmask32) __U); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_maskz_cvtne2ph_phf8 (__mmask32 __U, __m256h __A, __m256h __B) +_mm256_maskz_cvt2ph_hf8 (__mmask32 __U, __m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2hf8256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) - _mm256_setzero_si256 (), - (__mmask32) __U); + return (__m256i) __builtin_ia32_vcvt2ph2hf8256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) __U); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_cvtnes2ph_phf8 (__m128h __A, __m128h __B) +_mm_cvts2ph_hf8 (__m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2hf8s128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) - _mm_setzero_si128 (), - (__mmask16) -1); + return (__m128i) __builtin_ia32_vcvt2ph2hf8s128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) -1); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_mask_cvtnes2ph_phf8 (__m128i __W, __mmask16 __U, - __m128h __A, __m128h __B) +_mm_mask_cvts2ph_hf8 (__m128i __W, __mmask16 __U, + __m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2hf8s128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) __W, - (__mmask16) __U); + return (__m128i) __builtin_ia32_vcvt2ph2hf8s128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) __W, + (__mmask16) __U); } extern __inline__ __m128i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm_maskz_cvtnes2ph_phf8 (__mmask16 __U, __m128h __A, __m128h __B) +_mm_maskz_cvts2ph_hf8 (__mmask16 __U, __m128h __A, __m128h __B) { - return (__m128i) __builtin_ia32_vcvtne2ph2hf8s128_mask ((__v8hf) __A, - (__v8hf) __B, - (__v16qi) - _mm_setzero_si128 (), - (__mmask16) __U); + return (__m128i) __builtin_ia32_vcvt2ph2hf8s128_mask ((__v8hf) __A, + (__v8hf) __B, + (__v16qi) + _mm_setzero_si128 (), + (__mmask16) __U); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_cvtnes2ph_phf8 (__m256h __A, __m256h __B) +_mm256_cvts2ph_hf8 (__m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2hf8s256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) - _mm256_setzero_si256 (), - (__mmask32) -1); + return (__m256i) __builtin_ia32_vcvt2ph2hf8s256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) -1); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_mask_cvtnes2ph_phf8 (__m256i __W, __mmask32 __U, - __m256h __A, __m256h __B) +_mm256_mask_cvts2ph_hf8 (__m256i __W, __mmask32 __U, + __m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2hf8s256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) __W, - (__mmask32) __U); + return (__m256i) __builtin_ia32_vcvt2ph2hf8s256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) __W, + (__mmask32) __U); } extern __inline__ __m256i __attribute__ ((__gnu_inline__, __always_inline__, __artificial__)) -_mm256_maskz_cvtnes2ph_phf8 (__mmask32 __U, __m256h __A, __m256h __B) +_mm256_maskz_cvts2ph_hf8 (__mmask32 __U, __m256h __A, __m256h __B) { - return (__m256i) __builtin_ia32_vcvtne2ph2hf8s256_mask ((__v16hf) __A, - (__v16hf) __B, - (__v32qi) - _mm256_setzero_si256 (), - (__mmask32) __U); + return (__m256i) __builtin_ia32_vcvt2ph2hf8s256_mask ((__v16hf) __A, + (__v16hf) __B, + (__v32qi) + _mm256_setzero_si256 (), + (__mmask32) __U); } extern __inline__ __m128h diff --git a/gcc/config/i386/i386-builtin.def b/gcc/config/i386/i386-builtin.def index 7e1dad2615e..edd5c2b24d6 100644 --- a/gcc/config/i386/i386-builtin.def +++ b/gcc/config/i386/i386-builtin.def @@ -3152,18 +3152,18 @@ BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtbiasph2hf8sv8hf, "__builtin BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtbiasph2hf8sv8hf_mask, "__builtin_ia32_vcvtbiasph2hf8s128_mask", IX86_BUILTIN_VCVTBIASPH2HF8S128_MASK, UNKNOWN, (int) V16QI_FTYPE_V16QI_V8HF_V16QI_UHI) BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtbiasph2hf8sv16hf_mask, "__builtin_ia32_vcvtbiasph2hf8s256_mask", IX86_BUILTIN_VCVTBIASPH2HF8S256_MASK, UNKNOWN, (int) V16QI_FTYPE_V32QI_V16HF_V16QI_UHI) BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvtbiasph2hf8sv32hf_mask, "__builtin_ia32_vcvtbiasph2hf8s512_mask", IX86_BUILTIN_VCVTBIASPH2HF8S512_MASK, UNKNOWN, (int) V32QI_FTYPE_V64QI_V32HF_V32QI_USI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtne2ph2bf8v8hf_mask, "__builtin_ia32_vcvtne2ph2bf8128_mask", IX86_BUILTIN_VCVTNE2PH2BF8128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V8HF_V16QI_UHI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtne2ph2bf8v16hf_mask, "__builtin_ia32_vcvtne2ph2bf8256_mask", IX86_BUILTIN_VCVTNE2PH2BF8256_MASK, UNKNOWN, (int) V32QI_FTYPE_V16HF_V16HF_V32QI_USI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvtne2ph2bf8v32hf_mask, "__builtin_ia32_vcvtne2ph2bf8512_mask", IX86_BUILTIN_VCVTNE2PH2BF8512_MASK, UNKNOWN, (int) V64QI_FTYPE_V32HF_V32HF_V64QI_UDI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtne2ph2bf8sv8hf_mask, "__builtin_ia32_vcvtne2ph2bf8s128_mask", IX86_BUILTIN_VCVTNE2PH2BF8S128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V8HF_V16QI_UHI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtne2ph2bf8sv16hf_mask, "__builtin_ia32_vcvtne2ph2bf8s256_mask", IX86_BUILTIN_VCVTNE2PH2BF8S256_MASK, UNKNOWN, (int) V32QI_FTYPE_V16HF_V16HF_V32QI_USI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvtne2ph2bf8sv32hf_mask, "__builtin_ia32_vcvtne2ph2bf8s512_mask", IX86_BUILTIN_VCVTNE2PH2BF8S512_MASK, UNKNOWN, (int) V64QI_FTYPE_V32HF_V32HF_V64QI_UDI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtne2ph2hf8v8hf_mask, "__builtin_ia32_vcvtne2ph2hf8128_mask", IX86_BUILTIN_VCVTNE2PH2HF8128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V8HF_V16QI_UHI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtne2ph2hf8v16hf_mask, "__builtin_ia32_vcvtne2ph2hf8256_mask", IX86_BUILTIN_VCVTNE2PH2HF8256_MASK, UNKNOWN, (int) V32QI_FTYPE_V16HF_V16HF_V32QI_USI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvtne2ph2hf8v32hf_mask, "__builtin_ia32_vcvtne2ph2hf8512_mask", IX86_BUILTIN_VCVTNE2PH2HF8512_MASK, UNKNOWN, (int) V64QI_FTYPE_V32HF_V32HF_V64QI_UDI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtne2ph2hf8sv8hf_mask, "__builtin_ia32_vcvtne2ph2hf8s128_mask", IX86_BUILTIN_VCVTNE2PH2HF8S128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V8HF_V16QI_UHI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtne2ph2hf8sv16hf_mask, "__builtin_ia32_vcvtne2ph2hf8s256_mask", IX86_BUILTIN_VCVTNE2PH2HF8S256_MASK, UNKNOWN, (int) V32QI_FTYPE_V16HF_V16HF_V32QI_USI) -BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvtne2ph2hf8sv32hf_mask, "__builtin_ia32_vcvtne2ph2hf8s512_mask", IX86_BUILTIN_VCVTNE2PH2HF8S512_MASK, UNKNOWN, (int) V64QI_FTYPE_V32HF_V32HF_V64QI_UDI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvt2ph2bf8v8hf_mask, "__builtin_ia32_vcvt2ph2bf8128_mask", IX86_BUILTIN_VCVT2PH2BF8128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V8HF_V16QI_UHI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvt2ph2bf8v16hf_mask, "__builtin_ia32_vcvt2ph2bf8256_mask", IX86_BUILTIN_VCVT2PH2BF8256_MASK, UNKNOWN, (int) V32QI_FTYPE_V16HF_V16HF_V32QI_USI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvt2ph2bf8v32hf_mask, "__builtin_ia32_vcvt2ph2bf8512_mask", IX86_BUILTIN_VCVT2PH2BF8512_MASK, UNKNOWN, (int) V64QI_FTYPE_V32HF_V32HF_V64QI_UDI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvt2ph2bf8sv8hf_mask, "__builtin_ia32_vcvt2ph2bf8s128_mask", IX86_BUILTIN_VCVT2PH2BF8S128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V8HF_V16QI_UHI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvt2ph2bf8sv16hf_mask, "__builtin_ia32_vcvt2ph2bf8s256_mask", IX86_BUILTIN_VCVT2PH2BF8S256_MASK, UNKNOWN, (int) V32QI_FTYPE_V16HF_V16HF_V32QI_USI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvt2ph2bf8sv32hf_mask, "__builtin_ia32_vcvt2ph2bf8s512_mask", IX86_BUILTIN_VCVT2PH2BF8S512_MASK, UNKNOWN, (int) V64QI_FTYPE_V32HF_V32HF_V64QI_UDI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvt2ph2hf8v8hf_mask, "__builtin_ia32_vcvt2ph2hf8128_mask", IX86_BUILTIN_VCVT2PH2HF8128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V8HF_V16QI_UHI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvt2ph2hf8v16hf_mask, "__builtin_ia32_vcvt2ph2hf8256_mask", IX86_BUILTIN_VCVT2PH2HF8256_MASK, UNKNOWN, (int) V32QI_FTYPE_V16HF_V16HF_V32QI_USI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvt2ph2hf8v32hf_mask, "__builtin_ia32_vcvt2ph2hf8512_mask", IX86_BUILTIN_VCVT2PH2HF8512_MASK, UNKNOWN, (int) V64QI_FTYPE_V32HF_V32HF_V64QI_UDI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvt2ph2hf8sv8hf_mask, "__builtin_ia32_vcvt2ph2hf8s128_mask", IX86_BUILTIN_VCVT2PH2HF8S128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V8HF_V16QI_UHI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvt2ph2hf8sv16hf_mask, "__builtin_ia32_vcvt2ph2hf8s256_mask", IX86_BUILTIN_VCVT2PH2HF8S256_MASK, UNKNOWN, (int) V32QI_FTYPE_V16HF_V16HF_V32QI_USI) +BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvt2ph2hf8sv32hf_mask, "__builtin_ia32_vcvt2ph2hf8s512_mask", IX86_BUILTIN_VCVT2PH2HF8S512_MASK, UNKNOWN, (int) V64QI_FTYPE_V32HF_V32HF_V64QI_UDI) BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtneph2bf8v8hf_mask, "__builtin_ia32_vcvtneph2bf8128_mask", IX86_BUILTIN_VCVTNEPH2BF8128_MASK, UNKNOWN, (int) V16QI_FTYPE_V8HF_V16QI_UQI) BDESC (0, OPTION_MASK_ISA2_AVX10_2_256, CODE_FOR_vcvtneph2bf8v16hf_mask, "__builtin_ia32_vcvtneph2bf8256_mask", IX86_BUILTIN_VCVTNEPH2BF8256_MASK, UNKNOWN, (int) V16QI_FTYPE_V16HF_V16QI_UHI) BDESC (0, OPTION_MASK_ISA2_AVX10_2_512, CODE_FOR_vcvtneph2bf8v32hf_mask, "__builtin_ia32_vcvtneph2bf8512_mask", IX86_BUILTIN_VCVTNEPH2BF8512_MASK, UNKNOWN, (int) V32QI_FTYPE_V32HF_V32QI_USI) diff --git a/gcc/config/i386/sse.md b/gcc/config/i386/sse.md index c239f4102ae..582942cc20f 100644 --- a/gcc/config/i386/sse.md +++ b/gcc/config/i386/sse.md @@ -220,10 +220,10 @@ UNSPEC_VCVTBIASPH2BF8S UNSPEC_VCVTBIASPH2HF8 UNSPEC_VCVTBIASPH2HF8S - UNSPEC_VCVTNE2PH2BF8 - UNSPEC_VCVTNE2PH2BF8S - UNSPEC_VCVTNE2PH2HF8 - UNSPEC_VCVTNE2PH2HF8S + UNSPEC_VCVT2PH2BF8 + UNSPEC_VCVT2PH2BF8S + UNSPEC_VCVT2PH2HF8 + UNSPEC_VCVT2PH2HF8S UNSPEC_VCVTNEPH2BF8 UNSPEC_VCVTNEPH2BF8S UNSPEC_VCVTNEPH2HF8 @@ -31722,24 +31722,24 @@ (define_mode_attr ssebvecmode [(V8HF "V16QI") (V16HF "V32QI") (V32HF "V64QI")]) -(define_int_iterator UNSPEC_NECONVERTFP8_PACK - [UNSPEC_VCVTNE2PH2BF8 UNSPEC_VCVTNE2PH2BF8S - UNSPEC_VCVTNE2PH2HF8 UNSPEC_VCVTNE2PH2HF8S]) +(define_int_iterator UNSPEC_CONVERTFP8_PACK + [UNSPEC_VCVT2PH2BF8 UNSPEC_VCVT2PH2BF8S + UNSPEC_VCVT2PH2HF8 UNSPEC_VCVT2PH2HF8S]) -(define_int_attr neconvertfp8_pack - [(UNSPEC_VCVTNE2PH2BF8 "ne2ph2bf8") - (UNSPEC_VCVTNE2PH2BF8S "ne2ph2bf8s") - (UNSPEC_VCVTNE2PH2HF8 "ne2ph2hf8") - (UNSPEC_VCVTNE2PH2HF8S "ne2ph2hf8s")]) +(define_int_attr convertfp8_pack + [(UNSPEC_VCVT2PH2BF8 "2ph2bf8") + (UNSPEC_VCVT2PH2BF8S "2ph2bf8s") + (UNSPEC_VCVT2PH2HF8 "2ph2hf8") + (UNSPEC_VCVT2PH2HF8S "2ph2hf8s")]) -(define_insn "vcvt<neconvertfp8_pack><mode><mask_name>" +(define_insn "vcvt<convertfp8_pack><mode><mask_name>" [(set (match_operand:<ssebvecmode> 0 "register_operand" "=v") (unspec:<ssebvecmode> [(match_operand:VHF_AVX10_2 1 "register_operand" "v") (match_operand:VHF_AVX10_2 2 "nonimmediate_operand" "vm")] - UNSPEC_NECONVERTFP8_PACK))] + UNSPEC_CONVERTFP8_PACK))] "TARGET_AVX10_2_256" - "vcvt<neconvertfp8_pack>\t{%2, %1, %0<mask_operand3>|%0<mask_operand2>, %1, %2}" + "vcvt<convertfp8_pack>\t{%2, %1, %0<mask_operand3>|%0<mask_operand2>, %1, %2}" [(set_attr "prefix" "evex")]) (define_mode_attr ssebvecmode_2 diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-512-convert-1.c b/gcc/testsuite/gcc.target/i386/avx10_2-512-convert-1.c index 9a25e227589..955c862c486 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-512-convert-1.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-512-convert-1.c @@ -18,18 +18,18 @@ /* { dg-final { scan-assembler-times "vcvtbiasph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvtbiasph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvtbiasph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvthf82ph\[ \\t\]*%ymm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvthf82ph\[ \\t\]*%ymm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvthf82ph\[ \\t\]*%ymm\[0-9\]+,\[^\{\n\]*%zmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ @@ -108,35 +108,35 @@ avx10_2_512_vcvtbiasph2hf8s_test (void) } void extern -avx10_2_512_vcvtne2ph2bf8_test (void) +avx10_2_512_vcvt2ph2bf8_test (void) { - x512i = _mm512_cvtne2ph_pbf8 (x512h, x512h); - x512i = _mm512_mask_cvtne2ph_pbf8 (x512i, m64, x512h, x512h); - x512i = _mm512_maskz_cvtne2ph_pbf8 (m64, x512h, x512h); + x512i = _mm512_cvt2ph_bf8 (x512h, x512h); + x512i = _mm512_mask_cvt2ph_bf8 (x512i, m64, x512h, x512h); + x512i = _mm512_maskz_cvt2ph_bf8 (m64, x512h, x512h); } void extern -avx10_2_512_vcvtne2ph2bf8s_test (void) +avx10_2_512_vcvt2ph2bf8s_test (void) { - x512i = _mm512_cvtnes2ph_pbf8 (x512h, x512h); - x512i = _mm512_mask_cvtnes2ph_pbf8 (x512i, m64, x512h, x512h); - x512i = _mm512_maskz_cvtnes2ph_pbf8 (m64, x512h, x512h); + x512i = _mm512_cvts2ph_bf8 (x512h, x512h); + x512i = _mm512_mask_cvts2ph_bf8 (x512i, m64, x512h, x512h); + x512i = _mm512_maskz_cvts2ph_bf8 (m64, x512h, x512h); } void extern -avx10_2_512_vcvtne2ph2hf8_test (void) +avx10_2_512_vcvt2ph2hf8_test (void) { - x512i = _mm512_cvtne2ph_phf8 (x512h, x512h); - x512i = _mm512_mask_cvtne2ph_phf8 (x512i, m64, x512h, x512h); - x512i = _mm512_maskz_cvtne2ph_phf8 (m64, x512h, x512h); + x512i = _mm512_cvt2ph_hf8 (x512h, x512h); + x512i = _mm512_mask_cvt2ph_hf8 (x512i, m64, x512h, x512h); + x512i = _mm512_maskz_cvt2ph_hf8 (m64, x512h, x512h); } void extern -avx10_2_512_vcvtne2ph2hf8s_test (void) +avx10_2_512_vcvt2ph2hf8s_test (void) { - x512i = _mm512_cvtnes2ph_phf8 (x512h, x512h); - x512i = _mm512_mask_cvtnes2ph_phf8 (x512i, m64, x512h, x512h); - x512i = _mm512_maskz_cvtnes2ph_phf8 (m64, x512h, x512h); + x512i = _mm512_cvts2ph_hf8 (x512h, x512h); + x512i = _mm512_mask_cvts2ph_hf8 (x512i, m64, x512h, x512h); + x512i = _mm512_maskz_cvts2ph_hf8 (m64, x512h, x512h); } void extern diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2bf8-2.c b/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2bf8-2.c similarity index 89% rename from gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2bf8-2.c rename to gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2bf8-2.c index 7e7865d64fe..8662d26779c 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2bf8-2.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2bf8-2.c @@ -64,16 +64,16 @@ TEST (void) CALC(res_ref, src1.a, src2.a); - res1.x = INTRINSIC (_cvtne2ph_pbf8) (src1.x, src2.x); + res1.x = INTRINSIC (_cvt2ph_bf8) (src1.x, src2.x); if (UNION_CHECK (AVX512F_LEN, i_b) (res1, res_ref)) abort (); - res2.x = INTRINSIC (_mask_cvtne2ph_pbf8) (res2.x, mask, src1.x, src2.x); + res2.x = INTRINSIC (_mask_cvt2ph_bf8) (res2.x, mask, src1.x, src2.x); MASK_MERGE (i_b) (res_ref, mask, SIZE); if (UNION_CHECK (AVX512F_LEN, i_b) (res2, res_ref)) abort (); - res3.x = INTRINSIC (_maskz_cvtne2ph_pbf8) (mask, src1.x, src2.x); + res3.x = INTRINSIC (_maskz_cvt2ph_bf8) (mask, src1.x, src2.x); MASK_ZERO (i_b) (res_ref, mask, SIZE); if (UNION_CHECK (AVX512F_LEN, i_b) (res3, res_ref)) abort (); diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2bf8s-2.c b/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2bf8s-2.c similarity index 89% rename from gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2bf8s-2.c rename to gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2bf8s-2.c index 0ca0c420ff7..4933a8b8243 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2bf8s-2.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2bf8s-2.c @@ -64,16 +64,16 @@ TEST (void) CALC(res_ref, src1.a, src2.a); - res1.x = INTRINSIC (_cvtnes2ph_pbf8) (src1.x, src2.x); + res1.x = INTRINSIC (_cvts2ph_bf8) (src1.x, src2.x); if (UNION_CHECK (AVX512F_LEN, i_b) (res1, res_ref)) abort (); - res2.x = INTRINSIC (_mask_cvtnes2ph_pbf8) (res2.x, mask, src1.x, src2.x); + res2.x = INTRINSIC (_mask_cvts2ph_bf8) (res2.x, mask, src1.x, src2.x); MASK_MERGE (i_b) (res_ref, mask, SIZE); if (UNION_CHECK (AVX512F_LEN, i_b) (res2, res_ref)) abort (); - res3.x = INTRINSIC (_maskz_cvtnes2ph_pbf8) (mask, src1.x, src2.x); + res3.x = INTRINSIC (_maskz_cvts2ph_bf8) (mask, src1.x, src2.x); MASK_ZERO (i_b) (res_ref, mask, SIZE); if (UNION_CHECK (AVX512F_LEN, i_b) (res3, res_ref)) abort (); diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2hf8-2.c b/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2hf8-2.c similarity index 89% rename from gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2hf8-2.c rename to gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2hf8-2.c index 97afd395bb5..633d15aa3d5 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2hf8-2.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2hf8-2.c @@ -64,16 +64,16 @@ TEST (void) CALC(res_ref, src1.a, src2.a); - res1.x = INTRINSIC (_cvtne2ph_phf8) (src1.x, src2.x); + res1.x = INTRINSIC (_cvt2ph_hf8) (src1.x, src2.x); if (UNION_CHECK (AVX512F_LEN, i_b) (res1, res_ref)) abort (); - res2.x = INTRINSIC (_mask_cvtne2ph_phf8) (res2.x, mask, src1.x, src2.x); + res2.x = INTRINSIC (_mask_cvt2ph_hf8) (res2.x, mask, src1.x, src2.x); MASK_MERGE (i_b) (res_ref, mask, SIZE); if (UNION_CHECK (AVX512F_LEN, i_b) (res2, res_ref)) abort (); - res3.x = INTRINSIC (_maskz_cvtne2ph_phf8) (mask, src1.x, src2.x); + res3.x = INTRINSIC (_maskz_cvt2ph_hf8) (mask, src1.x, src2.x); MASK_ZERO (i_b) (res_ref, mask, SIZE); if (UNION_CHECK (AVX512F_LEN, i_b) (res3, res_ref)) abort (); diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2hf8s-2.c b/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2hf8s-2.c similarity index 89% rename from gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2hf8s-2.c rename to gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2hf8s-2.c index 2d99d11b023..e53e9242d13 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvtne2ph2hf8s-2.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-512-vcvt2ph2hf8s-2.c @@ -64,16 +64,16 @@ TEST (void) CALC(res_ref, src1.a, src2.a); - res1.x = INTRINSIC (_cvtnes2ph_phf8) (src1.x, src2.x); + res1.x = INTRINSIC (_cvts2ph_hf8) (src1.x, src2.x); if (UNION_CHECK (AVX512F_LEN, i_b) (res1, res_ref)) abort (); - res2.x = INTRINSIC (_mask_cvtnes2ph_phf8) (res2.x, mask, src1.x, src2.x); + res2.x = INTRINSIC (_mask_cvts2ph_hf8) (res2.x, mask, src1.x, src2.x); MASK_MERGE (i_b) (res_ref, mask, SIZE); if (UNION_CHECK (AVX512F_LEN, i_b) (res2, res_ref)) abort (); - res3.x = INTRINSIC (_maskz_cvtnes2ph_phf8) (mask, src1.x, src2.x); + res3.x = INTRINSIC (_maskz_cvts2ph_hf8) (mask, src1.x, src2.x); MASK_ZERO (i_b) (res_ref, mask, SIZE); if (UNION_CHECK (AVX512F_LEN, i_b) (res3, res_ref)) abort (); diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-convert-1.c b/gcc/testsuite/gcc.target/i386/avx10_2-convert-1.c index 190c9729ab7..49b34380e04 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-convert-1.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-convert-1.c @@ -33,30 +33,30 @@ /* { dg-final { scan-assembler-times "vcvtbiasph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvtbiasph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvtbiasph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2bf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ -/* { dg-final { scan-assembler-times "vcvtne2ph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2bf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ +/* { dg-final { scan-assembler-times "vcvt2ph2hf8s\[ \\t\]+\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+,\[^\{\n\]*%ymm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvthf82ph\[ \\t\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvthf82ph\[ \\t\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}(?:\n|\[ \\t\]+#)" 1 } } */ /* { dg-final { scan-assembler-times "vcvthf82ph\[ \\t\]*%xmm\[0-9\]+,\[^\{\n\]*%xmm\[0-9\]+\{%k\[1-7\]\}\{z\}(?:\n|\[ \\t\]+#)" 1 } } */ @@ -178,47 +178,47 @@ avx10_2_vcvtbiasph2hf8s_test (void) } void extern -avx10_2_vcvtne2ph2bf8_test (void) +avx10_2_vcvt2ph2bf8_test (void) { - x128i = _mm_cvtne2ph_pbf8 (x128h, x128h); - x128i = _mm_mask_cvtne2ph_pbf8 (x128i, m16, x128h, x128h); - x128i = _mm_maskz_cvtne2ph_pbf8 (m16, x128h, x128h); - x256i = _mm256_cvtne2ph_pbf8 (x256h, x256h); - x256i = _mm256_mask_cvtne2ph_pbf8 (x256i, m32, x256h, x256h); - x256i = _mm256_maskz_cvtne2ph_pbf8 (m32, x256h, x256h); + x128i = _mm_cvt2ph_bf8 (x128h, x128h); + x128i = _mm_mask_cvt2ph_bf8 (x128i, m16, x128h, x128h); + x128i = _mm_maskz_cvt2ph_bf8 (m16, x128h, x128h); + x256i = _mm256_cvt2ph_bf8 (x256h, x256h); + x256i = _mm256_mask_cvt2ph_bf8 (x256i, m32, x256h, x256h); + x256i = _mm256_maskz_cvt2ph_bf8 (m32, x256h, x256h); } void extern -avx10_2_vcvtne2ph2bf8s_test (void) +avx10_2_vcvt2ph2bf8s_test (void) { - x128i = _mm_cvtnes2ph_pbf8 (x128h, x128h); - x128i = _mm_mask_cvtnes2ph_pbf8 (x128i, m16, x128h, x128h); - x128i = _mm_maskz_cvtnes2ph_pbf8 (m16, x128h, x128h); - x256i = _mm256_cvtnes2ph_pbf8 (x256h, x256h); - x256i = _mm256_mask_cvtnes2ph_pbf8 (x256i, m32, x256h, x256h); - x256i = _mm256_maskz_cvtnes2ph_pbf8 (m32, x256h, x256h); + x128i = _mm_cvts2ph_bf8 (x128h, x128h); + x128i = _mm_mask_cvts2ph_bf8 (x128i, m16, x128h, x128h); + x128i = _mm_maskz_cvts2ph_bf8 (m16, x128h, x128h); + x256i = _mm256_cvts2ph_bf8 (x256h, x256h); + x256i = _mm256_mask_cvts2ph_bf8 (x256i, m32, x256h, x256h); + x256i = _mm256_maskz_cvts2ph_bf8 (m32, x256h, x256h); } void extern -avx10_2_vcvtne2ph2hf8_test (void) +avx10_2_vcvt2ph2hf8_test (void) { - x128i = _mm_cvtne2ph_phf8 (x128h, x128h); - x128i = _mm_mask_cvtne2ph_phf8 (x128i, m16, x128h, x128h); - x128i = _mm_maskz_cvtne2ph_phf8 (m16, x128h, x128h); - x256i = _mm256_cvtne2ph_phf8 (x256h, x256h); - x256i = _mm256_mask_cvtne2ph_phf8 (x256i, m32, x256h, x256h); - x256i = _mm256_maskz_cvtne2ph_phf8 (m32, x256h, x256h); + x128i = _mm_cvt2ph_hf8 (x128h, x128h); + x128i = _mm_mask_cvt2ph_hf8 (x128i, m16, x128h, x128h); + x128i = _mm_maskz_cvt2ph_hf8 (m16, x128h, x128h); + x256i = _mm256_cvt2ph_hf8 (x256h, x256h); + x256i = _mm256_mask_cvt2ph_hf8 (x256i, m32, x256h, x256h); + x256i = _mm256_maskz_cvt2ph_hf8 (m32, x256h, x256h); } void extern -avx10_2_vcvtne2ph2hf8s_test (void) +avx10_2_vcvt2ph2hf8s_test (void) { - x128i = _mm_cvtnes2ph_phf8 (x128h, x128h); - x128i = _mm_mask_cvtnes2ph_phf8 (x128i, m16, x128h, x128h); - x128i = _mm_maskz_cvtnes2ph_phf8 (m16, x128h, x128h); - x256i = _mm256_cvtnes2ph_phf8 (x256h, x256h); - x256i = _mm256_mask_cvtnes2ph_phf8 (x256i, m32, x256h, x256h); - x256i = _mm256_maskz_cvtnes2ph_phf8 (m32, x256h, x256h); + x128i = _mm_cvts2ph_hf8 (x128h, x128h); + x128i = _mm_mask_cvts2ph_hf8 (x128i, m16, x128h, x128h); + x128i = _mm_maskz_cvts2ph_hf8 (m16, x128h, x128h); + x256i = _mm256_cvts2ph_hf8 (x256h, x256h); + x256i = _mm256_mask_cvts2ph_hf8 (x256i, m32, x256h, x256h); + x256i = _mm256_maskz_cvts2ph_hf8 (m32, x256h, x256h); } void extern diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2bf8-2.c b/gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2bf8-2.c similarity index 78% rename from gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2bf8-2.c rename to gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2bf8-2.c index bf1a6c86000..9dd940ce766 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2bf8-2.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2bf8-2.c @@ -6,11 +6,11 @@ #define AVX512VL #define AVX512F_LEN 256 #define AVX512F_LEN_HALF 128 -#include "avx10_2-512-vcvtne2ph2bf8-2.c" +#include "avx10_2-512-vcvt2ph2bf8-2.c" #undef AVX512F_LEN #undef AVX512F_LEN_HALF #define AVX512F_LEN 128 #define AVX512F_LEN_HALF 128 -#include "avx10_2-512-vcvtne2ph2bf8-2.c" +#include "avx10_2-512-vcvt2ph2bf8-2.c" diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2hf8-2.c b/gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2bf8s-2.c similarity index 78% rename from gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2hf8-2.c rename to gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2bf8s-2.c index 6a2db562957..2a9caca57d0 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2hf8-2.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2bf8s-2.c @@ -6,11 +6,11 @@ #define AVX512VL #define AVX512F_LEN 256 #define AVX512F_LEN_HALF 128 -#include "avx10_2-512-vcvtne2ph2hf8-2.c" +#include "avx10_2-512-vcvt2ph2bf8s-2.c" #undef AVX512F_LEN #undef AVX512F_LEN_HALF #define AVX512F_LEN 128 #define AVX512F_LEN_HALF 128 -#include "avx10_2-512-vcvtne2ph2hf8-2.c" +#include "avx10_2-512-vcvt2ph2bf8s-2.c" diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2bf8s-2.c b/gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2hf8-2.c similarity index 78% rename from gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2bf8s-2.c rename to gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2hf8-2.c index e02b7ec2959..80dc2480867 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2bf8s-2.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2hf8-2.c @@ -6,11 +6,11 @@ #define AVX512VL #define AVX512F_LEN 256 #define AVX512F_LEN_HALF 128 -#include "avx10_2-512-vcvtne2ph2bf8s-2.c" +#include "avx10_2-512-vcvt2ph2hf8-2.c" #undef AVX512F_LEN #undef AVX512F_LEN_HALF #define AVX512F_LEN 128 #define AVX512F_LEN_HALF 128 -#include "avx10_2-512-vcvtne2ph2bf8s-2.c" +#include "avx10_2-512-vcvt2ph2hf8-2.c" diff --git a/gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2hf8s-2.c b/gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2hf8s-2.c similarity index 78% rename from gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2hf8s-2.c rename to gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2hf8s-2.c index 20415276eea..30f6a6075cf 100644 --- a/gcc/testsuite/gcc.target/i386/avx10_2-vcvtne2ph2hf8s-2.c +++ b/gcc/testsuite/gcc.target/i386/avx10_2-vcvt2ph2hf8s-2.c @@ -6,11 +6,11 @@ #define AVX512VL #define AVX512F_LEN 256 #define AVX512F_LEN_HALF 128 -#include "avx10_2-512-vcvtne2ph2hf8s-2.c" +#include "avx10_2-512-vcvt2ph2hf8s-2.c" #undef AVX512F_LEN #undef AVX512F_LEN_HALF #define AVX512F_LEN 128 #define AVX512F_LEN_HALF 128 -#include "avx10_2-512-vcvtne2ph2hf8s-2.c" +#include "avx10_2-512-vcvt2ph2hf8s-2.c" -- 2.31.1