Skip to content

Commit

Permalink
[SYCLomatic] Update intrinsic and mnemonics names
Browse files Browse the repository at this point in the history 
Signed-off-by: chenwei.sun <[email protected]>
  • Loading branch information
@tomflinda
tomflinda committed Feb 26, 2025
1 parent 87a5336 commit 20b94f0
Show file tree
Hide file tree
Showing 27 changed files with 1,153 additions and 1,153 deletions.
18 changes: 9 additions & 9 deletions clang/include/clang/Basic/BuiltinsX86.def
View file
Original file line number Diff line number Diff line change
Expand Up @@ -2215,12 +2215,12 @@ TARGET_BUILTIN(__builtin_ia32_vcvtps2ibs512_mask, "V16UiV16fV16UiUsIi", "nV:512:
TARGET_BUILTIN(__builtin_ia32_vcvtps2iubs128_mask, "V4UiV4fV4UiUc", "nV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvtps2iubs256_mask, "V8UiV8fV8UiUcIi", "nV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvtps2iubs512_mask, "V16UiV16fV16UiUsIi", "nV:512:", "avx10.2-512")
TARGET_BUILTIN(__builtin_ia32_vcvttnebf162ibs128, "V8UsV8y", "nV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttnebf162ibs256, "V16UsV16y", "nV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttnebf162ibs512, "V32UsV32y", "nV:512:", "avx10.2-512")
TARGET_BUILTIN(__builtin_ia32_vcvttnebf162iubs128, "V8UsV8y", "nV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttnebf162iubs256, "V16UsV16y", "nV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttnebf162iubs512, "V32UsV32y", "nV:512:", "avx10.2-512")
TARGET_BUILTIN(__builtin_ia32_vcvttbf162ibs128, "V8UsV8y", "nV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttbf162ibs256, "V16UsV16y", "nV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttbf162ibs512, "V32UsV32y", "nV:512:", "avx10.2-512")
TARGET_BUILTIN(__builtin_ia32_vcvttbf162iubs128, "V8UsV8y", "nV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttbf162iubs256, "V16UsV16y", "nV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttbf162iubs512, "V32UsV32y", "nV:512:", "avx10.2-512")
TARGET_BUILTIN(__builtin_ia32_vcvttph2ibs128_mask, "V8UsV8xV8UsUc", "nV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttph2ibs256_mask, "V16UsV16xV16UsUsIi", "nV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vcvttph2ibs512_mask, "V32UsV32xV32UsUiIi", "nV:512:", "avx10.2-512")
Expand Down Expand Up @@ -2311,9 +2311,9 @@ TARGET_BUILTIN(__builtin_ia32_vcmpbf16128_mask,"UcV8yV8yIiUc", "ncV:128:", "avx1
TARGET_BUILTIN(__builtin_ia32_vfpclassbf16128_mask, "UcV8yIiUc", "ncV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vfpclassbf16256_mask, "UsV16yIiUs", "ncV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vfpclassbf16512_mask, "UiV32yIiUi", "ncV:512:", "avx10.2-512")
TARGET_BUILTIN(__builtin_ia32_vscalefpbf16128_mask, "V8yV8yV8yV8yUc", "ncV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vscalefpbf16256_mask, "V16yV16yV16yV16yUs", "ncV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vscalefpbf16512_mask, "V32yV32yV32yV32yUi", "ncV:512:", "avx10.2-512")
TARGET_BUILTIN(__builtin_ia32_vscalefbf16128_mask, "V8yV8yV8yV8yUc", "ncV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vscalefbf16256_mask, "V16yV16yV16yV16yUs", "ncV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vscalefbf16512_mask, "V32yV32yV32yV32yUi", "ncV:512:", "avx10.2-512")
TARGET_BUILTIN(__builtin_ia32_vrcpbf16128_mask, "V8yV8yV8yUc", "ncV:128:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vrcpbf16256_mask, "V16yV16yV16yUs", "ncV:256:", "avx10.2-256")
TARGET_BUILTIN(__builtin_ia32_vrcpbf16512_mask, "V32yV32yV32yUi", "ncV:512:", "avx10.2-512")
Expand Down
6 changes: 3 additions & 3 deletions clang/lib/Headers/avx10_2_512bf16intrin.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -306,20 +306,20 @@ _mm512_maskz_min_pbh(__mmask32 __U, __m512bh __A, __m512bh __B) {

static __inline__ __m512bh __DEFAULT_FN_ATTRS512
_mm512_scalef_pbh(__m512bh __A, __m512bh __B) {
return (__m512bh)__builtin_ia32_vscalefpbf16512_mask(
return (__m512bh)__builtin_ia32_vscalefbf16512_mask(
(__v32bf)__A, (__v32bf)__B, (__v32bf)_mm512_undefined_pbh(),
(__mmask32)-1);
}

static __inline__ __m512bh __DEFAULT_FN_ATTRS512 _mm512_mask_scalef_pbh(
__m512bh __W, __mmask32 __U, __m512bh __A, __m512bh __B) {
return (__m512bh)__builtin_ia32_vscalefpbf16512_mask(
return (__m512bh)__builtin_ia32_vscalefbf16512_mask(
(__v32bf)__A, (__v32bf)__B, (__v32bf)__W, (__mmask32)__U);
}

static __inline__ __m512bh __DEFAULT_FN_ATTRS512
_mm512_maskz_scalef_pbh(__mmask32 __U, __m512bh __A, __m512bh __B) {
return (__m512bh)__builtin_ia32_vscalefpbf16512_mask(
return (__m512bh)__builtin_ia32_vscalefbf16512_mask(
(__v32bf)__A, (__v32bf)__B, (__v32bf)_mm512_setzero_pbh(),
(__mmask32)__U);
}
Expand Down
4 changes: 2 additions & 2 deletions clang/lib/Headers/avx10_2_512satcvtintrin.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -41,7 +41,7 @@
(__v32hi)_mm512_setzero_si512()))

#define _mm512_ipcvttnebf16_epi8(A) \
((__m512i)__builtin_ia32_vcvttnebf162ibs512((__v32bf)(__m512bh)(A)))
((__m512i)__builtin_ia32_vcvttbf162ibs512((__v32bf)(__m512bh)(A)))

#define _mm512_mask_ipcvttnebf16_epi8(W, U, A) \
((__m512i)__builtin_ia32_selectw_512((__mmask32)(U), \
Expand All @@ -54,7 +54,7 @@
(__v32hi)_mm512_setzero_si512()))

#define _mm512_ipcvttnebf16_epu8(A) \
((__m512i)__builtin_ia32_vcvttnebf162iubs512((__v32bf)(__m512bh)(A)))
((__m512i)__builtin_ia32_vcvttbf162iubs512((__v32bf)(__m512bh)(A)))

#define _mm512_mask_ipcvttnebf16_epu8(W, U, A) \
((__m512i)__builtin_ia32_selectw_512((__mmask32)(U), \
Expand Down
12 changes: 6 additions & 6 deletions clang/lib/Headers/avx10_2bf16intrin.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -591,39 +591,39 @@ static __inline__ int __DEFAULT_FN_ATTRS128 _mm_comneqsbh(__m128bh A,

static __inline__ __m256bh __DEFAULT_FN_ATTRS256
_mm256_scalef_pbh(__m256bh __A, __m256bh __B) {
return (__m256bh)__builtin_ia32_vscalefpbf16256_mask(
return (__m256bh)__builtin_ia32_vscalefbf16256_mask(
(__v16bf)__A, (__v16bf)__B, (__v16bf)_mm256_undefined_pbh(),
(__mmask16)-1);
}

static __inline__ __m256bh __DEFAULT_FN_ATTRS256 _mm256_mask_scalef_pbh(
__m256bh __W, __mmask16 __U, __m256bh __A, __m256bh __B) {
return (__m256bh)__builtin_ia32_vscalefpbf16256_mask(
return (__m256bh)__builtin_ia32_vscalefbf16256_mask(
(__v16bf)__A, (__v16bf)__B, (__v16bf)__W, (__mmask16)__U);
}

static __inline__ __m256bh __DEFAULT_FN_ATTRS256
_mm256_maskz_scalef_pbh(__mmask16 __U, __m256bh __A, __m256bh __B) {
return (__m256bh)__builtin_ia32_vscalefpbf16256_mask(
return (__m256bh)__builtin_ia32_vscalefbf16256_mask(
(__v16bf)__A, (__v16bf)__B, (__v16bf)_mm256_setzero_pbh(),
(__mmask16)__U);
}

static __inline__ __m128bh __DEFAULT_FN_ATTRS128 _mm_scalef_pbh(__m128bh __A,
__m128bh __B) {
return (__m128bh)__builtin_ia32_vscalefpbf16128_mask(
return (__m128bh)__builtin_ia32_vscalefbf16128_mask(
(__v8bf)__A, (__v8bf)__B, (__v8bf)_mm_undefined_pbh(), (__mmask8)-1);
}

static __inline__ __m128bh __DEFAULT_FN_ATTRS128
_mm_mask_scalef_pbh(__m128bh __W, __mmask8 __U, __m128bh __A, __m128bh __B) {
return (__m128bh)__builtin_ia32_vscalefpbf16128_mask(
return (__m128bh)__builtin_ia32_vscalefbf16128_mask(
(__v8bf)__A, (__v8bf)__B, (__v8bf)__W, (__mmask8)__U);
}

static __inline__ __m128bh __DEFAULT_FN_ATTRS128
_mm_maskz_scalef_pbh(__mmask8 __U, __m128bh __A, __m128bh __B) {
return (__m128bh)__builtin_ia32_vscalefpbf16128_mask(
return (__m128bh)__builtin_ia32_vscalefbf16128_mask(
(__v8bf)__A, (__v8bf)__B, (__v8bf)_mm_setzero_pbh(), (__mmask8)__U);
}

Expand Down
8 changes: 4 additions & 4 deletions clang/lib/Headers/avx10_2satcvtintrin.h
View file
Original file line number Diff line number Diff line change
Expand Up @@ -229,7 +229,7 @@
(__mmask8)(U), (const int)R))

#define _mm_ipcvttnebf16_epi8(A) \
((__m128i)__builtin_ia32_vcvttnebf162ibs128((__v8bf)(__m128bh)(A)))
((__m128i)__builtin_ia32_vcvttbf162ibs128((__v8bf)(__m128bh)(A)))

#define _mm_mask_ipcvttnebf16_epi8(W, U, A) \
((__m128i)__builtin_ia32_selectw_128( \
Expand All @@ -241,7 +241,7 @@
(__v8hi)_mm_setzero_si128()))

#define _mm256_ipcvttnebf16_epi8(A) \
((__m256i)__builtin_ia32_vcvttnebf162ibs256((__v16bf)(__m256bh)(A)))
((__m256i)__builtin_ia32_vcvttbf162ibs256((__v16bf)(__m256bh)(A)))

#define _mm256_mask_ipcvttnebf16_epi8(W, U, A) \
((__m256i)__builtin_ia32_selectw_256((__mmask16)(U), \
Expand All @@ -254,7 +254,7 @@
(__v16hi)_mm256_setzero_si256()))

#define _mm_ipcvttnebf16_epu8(A) \
((__m128i)__builtin_ia32_vcvttnebf162iubs128((__v8bf)(__m128bh)(A)))
((__m128i)__builtin_ia32_vcvttbf162iubs128((__v8bf)(__m128bh)(A)))

#define _mm_mask_ipcvttnebf16_epu8(W, U, A) \
((__m128i)__builtin_ia32_selectw_128( \
Expand All @@ -266,7 +266,7 @@
(__v8hi)_mm_setzero_si128()))

#define _mm256_ipcvttnebf16_epu8(A) \
((__m256i)__builtin_ia32_vcvttnebf162iubs256((__v16bf)(__m256bh)(A)))
((__m256i)__builtin_ia32_vcvttbf162iubs256((__v16bf)(__m256bh)(A)))

#define _mm256_mask_ipcvttnebf16_epu8(W, U, A) \
((__m256i)__builtin_ia32_selectw_256((__mmask16)(U), \
Expand Down
12 changes: 6 additions & 6 deletions clang/test/CodeGen/X86/avx10_2_512satcvt-builtins.c
View file
Original file line number Diff line number Diff line change
Expand Up @@ -193,41 +193,41 @@ __m512i test_mm512_maskz_ipcvt_roundps_epu8(__mmask16 __A, __m512 __B) {

__m512i test_mm512_ipcvttnebf16_epi8(__m512bh __A) {
// CHECK-LABEL: @test_mm512_ipcvttnebf16_epi8(
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs512(
// CHECK: @llvm.x86.avx10.vcvttbf162ibs512(
return _mm512_ipcvttnebf16_epi8(__A);
}

__m512i test_mm512_mask_ipcvttnebf16_epi8(__m512i __S, __mmask32 __A, __m512bh __B) {
// CHECK-LABEL: @test_mm512_mask_ipcvttnebf16_epi8(
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs512(
// CHECK: @llvm.x86.avx10.vcvttbf162ibs512(
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_mask_ipcvttnebf16_epi8(__S, __A, __B);
}

__m512i test_mm512_maskz_ipcvttnebf16_epi8(__mmask32 __A, __m512bh __B) {
// CHECK-LABEL: @test_mm512_maskz_ipcvttnebf16_epi8
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs512(
// CHECK: @llvm.x86.avx10.vcvttbf162ibs512(
// CHECK: zeroinitializer
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_maskz_ipcvttnebf16_epi8(__A, __B);
}

__m512i test_mm512_ipcvttnebf16_epu8(__m512bh __A) {
// CHECK-LABEL: @test_mm512_ipcvttnebf16_epu8(
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs512(
// CHECK: @llvm.x86.avx10.vcvttbf162iubs512(
return _mm512_ipcvttnebf16_epu8(__A);
}

__m512i test_mm512_mask_ipcvttnebf16_epu8(__m512i __S, __mmask32 __A, __m512bh __B) {
// CHECK-LABEL: @test_mm512_mask_ipcvttnebf16_epu8(
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs512(
// CHECK: @llvm.x86.avx10.vcvttbf162iubs512(
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_mask_ipcvttnebf16_epu8(__S, __A, __B);
}

__m512i test_mm512_maskz_ipcvttnebf16_epu8(__mmask32 __A, __m512bh __B) {
// CHECK-LABEL: @test_mm512_maskz_ipcvttnebf16_epu8
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs512(
// CHECK: @llvm.x86.avx10.vcvttbf162iubs512(
// CHECK: zeroinitializer
// CHECK: select <32 x i1> %{{.*}}, <32 x i16> %{{.*}}, <32 x i16> %{{.*}}
return _mm512_maskz_ipcvttnebf16_epu8(__A, __B);
Expand Down
24 changes: 12 additions & 12 deletions clang/test/CodeGen/X86/avx10_2satcvt-builtins.c
View file
Original file line number Diff line number Diff line change
Expand Up @@ -304,83 +304,83 @@ __m256i test_mm256_maskz_ipcvt_roundps_epu8(__mmask8 __A, __m256 __B) {

__m128i test_mm_ipcvttnebf16_epi8(__m128bh __A) {
// CHECK-LABEL: @test_mm_ipcvttnebf16_epi8(
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs128
// CHECK: @llvm.x86.avx10.vcvttbf162ibs128
return _mm_ipcvttnebf16_epi8(__A);
}

__m128i test_mm_mask_ipcvttnebf16_epi8(__m128i __S, __mmask8 __A, __m128bh __B) {
// CHECK-LABEL: @test_mm_mask_ipcvttnebf16_epi8(
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs128
// CHECK: @llvm.x86.avx10.vcvttbf162ibs128
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_mask_ipcvttnebf16_epi8(__S, __A, __B);
}

__m128i test_mm_maskz_ipcvttnebf16_epi8(__mmask8 __A, __m128bh __B) {
// CHECK-LABEL: @test_mm_maskz_ipcvttnebf16_epi8(
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs128
// CHECK: @llvm.x86.avx10.vcvttbf162ibs128
// CHECK: zeroinitializer
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_maskz_ipcvttnebf16_epi8(__A, __B);
}

__m256i test_mm256_ipcvttnebf16_epi8(__m256bh __A) {
// CHECK-LABEL: @test_mm256_ipcvttnebf16_epi8(
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs256
// CHECK: @llvm.x86.avx10.vcvttbf162ibs256
return _mm256_ipcvttnebf16_epi8(__A);
}

__m256i test_mm256_mask_ipcvttnebf16_epi8(__m256i __S, __mmask16 __A, __m256bh __B) {
// CHECK-LABEL: @test_mm256_mask_ipcvttnebf16_epi8(
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs256
// CHECK: @llvm.x86.avx10.vcvttbf162ibs256
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_mask_ipcvttnebf16_epi8(__S, __A, __B);
}

__m256i test_mm256_maskz_ipcvttnebf16_epi8(__mmask16 __A, __m256bh __B) {
// CHECK-LABEL: @test_mm256_maskz_ipcvttnebf16_epi8(
// CHECK: @llvm.x86.avx10.vcvttnebf162ibs256
// CHECK: @llvm.x86.avx10.vcvttbf162ibs256
// CHECK: zeroinitializer
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_maskz_ipcvttnebf16_epi8(__A, __B);
}

__m128i test_mm_ipcvttnebf16_epu8(__m128bh __A) {
// CHECK-LABEL: @test_mm_ipcvttnebf16_epu8(
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs128
// CHECK: @llvm.x86.avx10.vcvttbf162iubs128
return _mm_ipcvttnebf16_epu8(__A);
}

__m128i test_mm_mask_ipcvttnebf16_epu8(__m128i __S, __mmask8 __A, __m128bh __B) {
// CHECK-LABEL: @test_mm_mask_ipcvttnebf16_epu8(
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs128
// CHECK: @llvm.x86.avx10.vcvttbf162iubs128
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_mask_ipcvttnebf16_epu8(__S, __A, __B);
}

__m128i test_mm_maskz_ipcvttnebf16_epu8(__mmask8 __A, __m128bh __B) {
// CHECK-LABEL: @test_mm_maskz_ipcvttnebf16_epu8(
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs128
// CHECK: @llvm.x86.avx10.vcvttbf162iubs128
// CHECK: zeroinitializer
// CHECK: select <8 x i1> %{{.*}}, <8 x i16> %{{.*}}, <8 x i16> %{{.*}}
return _mm_maskz_ipcvttnebf16_epu8(__A, __B);
}

__m256i test_mm256_ipcvttnebf16_epu8(__m256bh __A) {
// CHECK-LABEL: @test_mm256_ipcvttnebf16_epu8(
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs256
// CHECK: @llvm.x86.avx10.vcvttbf162iubs256
return _mm256_ipcvttnebf16_epu8(__A);
}

__m256i test_mm256_mask_ipcvttnebf16_epu8(__m256i __S, __mmask16 __A, __m256bh __B) {
// CHECK-LABEL: @test_mm256_mask_ipcvttnebf16_epu8(
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs256
// CHECK: @llvm.x86.avx10.vcvttbf162iubs256
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_mask_ipcvttnebf16_epu8(__S, __A, __B);
}

__m256i test_mm256_maskz_ipcvttnebf16_epu8(__mmask16 __A, __m256bh __B) {
// CHECK-LABEL: @test_mm256_maskz_ipcvttnebf16_epu8(
// CHECK: @llvm.x86.avx10.vcvttnebf162iubs256
// CHECK: @llvm.x86.avx10.vcvttbf162iubs256
// CHECK: zeroinitializer
// CHECK: select <16 x i1> %{{.*}}, <16 x i16> %{{.*}}, <16 x i16> %{{.*}}
return _mm256_maskz_ipcvttnebf16_epu8(__A, __B);
Expand Down
18 changes: 9 additions & 9 deletions llvm/include/llvm/IR/IntrinsicsX86.td
View file
Original file line number Diff line number Diff line change
Expand Up @@ -7134,22 +7134,22 @@ def int_x86_avx10_mask_vcvtps2iubs256 : ClangBuiltin<"__builtin_ia32_vcvtps2iubs
def int_x86_avx10_mask_vcvtps2iubs512 : ClangBuiltin<"__builtin_ia32_vcvtps2iubs512_mask">,
DefaultAttrsIntrinsic<[llvm_v16i32_ty], [llvm_v16f32_ty, llvm_v16i32_ty, llvm_i16_ty, llvm_i32_ty],
[IntrNoMem, ImmArg<ArgIndex<3>>]>;
def int_x86_avx10_vcvttnebf162ibs128 : ClangBuiltin<"__builtin_ia32_vcvttnebf162ibs128">,
def int_x86_avx10_vcvttbf162ibs128 : ClangBuiltin<"__builtin_ia32_vcvttbf162ibs128">,
DefaultAttrsIntrinsic<[llvm_v8i16_ty], [llvm_v8bf16_ty],
[IntrNoMem]>;
def int_x86_avx10_vcvttnebf162ibs256 : ClangBuiltin<"__builtin_ia32_vcvttnebf162ibs256">,
def int_x86_avx10_vcvttbf162ibs256 : ClangBuiltin<"__builtin_ia32_vcvttbf162ibs256">,
DefaultAttrsIntrinsic<[llvm_v16i16_ty], [llvm_v16bf16_ty],
[IntrNoMem]>;
def int_x86_avx10_vcvttnebf162ibs512 : ClangBuiltin<"__builtin_ia32_vcvttnebf162ibs512">,
def int_x86_avx10_vcvttbf162ibs512 : ClangBuiltin<"__builtin_ia32_vcvttbf162ibs512">,
DefaultAttrsIntrinsic<[llvm_v32i16_ty], [llvm_v32bf16_ty],
[IntrNoMem]>;
def int_x86_avx10_vcvttnebf162iubs128 : ClangBuiltin<"__builtin_ia32_vcvttnebf162iubs128">,
def int_x86_avx10_vcvttbf162iubs128 : ClangBuiltin<"__builtin_ia32_vcvttbf162iubs128">,
DefaultAttrsIntrinsic<[llvm_v8i16_ty], [llvm_v8bf16_ty],
[IntrNoMem]>;
def int_x86_avx10_vcvttnebf162iubs256 : ClangBuiltin<"__builtin_ia32_vcvttnebf162iubs256">,
def int_x86_avx10_vcvttbf162iubs256 : ClangBuiltin<"__builtin_ia32_vcvttbf162iubs256">,
DefaultAttrsIntrinsic<[llvm_v16i16_ty], [llvm_v16bf16_ty],
[IntrNoMem]>;
def int_x86_avx10_vcvttnebf162iubs512 : ClangBuiltin<"__builtin_ia32_vcvttnebf162iubs512">,
def int_x86_avx10_vcvttbf162iubs512 : ClangBuiltin<"__builtin_ia32_vcvttbf162iubs512">,
DefaultAttrsIntrinsic<[llvm_v32i16_ty], [llvm_v32bf16_ty],
[IntrNoMem]>;
def int_x86_avx10_mask_vcvttph2ibs128 : ClangBuiltin<"__builtin_ia32_vcvttph2ibs128_mask">,
Expand Down Expand Up @@ -7457,13 +7457,13 @@ def int_x86_avx10_mask_rndscale_bf16_256 : ClangBuiltin<"__builtin_ia32_vrndscal
def int_x86_avx10_mask_rndscale_bf16_512 : ClangBuiltin<"__builtin_ia32_vrndscalebf16_mask">,
DefaultAttrsIntrinsic<[llvm_v32bf16_ty], [llvm_v32bf16_ty, llvm_i32_ty, llvm_v32bf16_ty, llvm_i32_ty],
[IntrNoMem, ImmArg<ArgIndex<1>>]>;
def int_x86_avx10_mask_scalef_bf16_128 : ClangBuiltin<"__builtin_ia32_vscalefpbf16128_mask">,
def int_x86_avx10_mask_scalef_bf16_128 : ClangBuiltin<"__builtin_ia32_vscalefbf16128_mask">,
DefaultAttrsIntrinsic<[llvm_v8bf16_ty], [llvm_v8bf16_ty, llvm_v8bf16_ty, llvm_v8bf16_ty, llvm_i8_ty],
[IntrNoMem]>;
def int_x86_avx10_mask_scalef_bf16_256 : ClangBuiltin<"__builtin_ia32_vscalefpbf16256_mask">,
def int_x86_avx10_mask_scalef_bf16_256 : ClangBuiltin<"__builtin_ia32_vscalefbf16256_mask">,
DefaultAttrsIntrinsic<[llvm_v16bf16_ty], [llvm_v16bf16_ty, llvm_v16bf16_ty, llvm_v16bf16_ty, llvm_i16_ty],
[IntrNoMem]>;
def int_x86_avx10_mask_scalef_bf16_512 : ClangBuiltin<"__builtin_ia32_vscalefpbf16512_mask">,
def int_x86_avx10_mask_scalef_bf16_512 : ClangBuiltin<"__builtin_ia32_vscalefbf16512_mask">,
DefaultAttrsIntrinsic<[llvm_v32bf16_ty], [llvm_v32bf16_ty, llvm_v32bf16_ty, llvm_v32bf16_ty, llvm_i32_ty],
[IntrNoMem]>;
def int_x86_avx10_vfmadd213bf16256 : ClangBuiltin<"__builtin_ia32_vfmadd213bf16256">,
Expand Down
Loading

0 comments on commit 20b94f0

Please sign in to comment.