Skip to content

Commit 13c6abf

Browse files
phoebewangphoebewang
authored
[X86][AVX10.2-MINMAX][NFC] Remove NE[P] from intrinsic and instruction (#123272)
Ref.: https://cdrdv2.intel.com/v1/dl/getContent/828965
1 parent c7de642 commit 13c6abf

21 files changed

+490
-493
lines changed

‎clang/include/clang/Basic/BuiltinsX86.td‎

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -4936,15 +4936,15 @@ let Features = "avx10.2-512,sm4", Attributes = [NoThrow, RequiredVectorWidth<512
49364936
}
49374937

49384938
let Features = "avx10.2-256", Attributes = [NoThrow, RequiredVectorWidth<128>] in {
4939-
def vminmaxnepbf16128 : X86Builtin<"_Vector<8, __bf16>(_Vector<8, __bf16>, _Vector<8, __bf16>, _Constant int)">;
4939+
def vminmaxbf16128 : X86Builtin<"_Vector<8, __bf16>(_Vector<8, __bf16>, _Vector<8, __bf16>, _Constant int)">;
49404940
}
49414941

49424942
let Features = "avx10.2-256", Attributes = [NoThrow, RequiredVectorWidth<256>] in {
4943-
def vminmaxnepbf16256 : X86Builtin<"_Vector<16, __bf16>(_Vector<16, __bf16>, _Vector<16, __bf16>, _Constant int)">;
4943+
def vminmaxbf16256 : X86Builtin<"_Vector<16, __bf16>(_Vector<16, __bf16>, _Vector<16, __bf16>, _Constant int)">;
49444944
}
49454945

49464946
let Features = "avx10.2-512", Attributes = [NoThrow, RequiredVectorWidth<512>] in {
4947-
def vminmaxnepbf16512 : X86Builtin<"_Vector<32, __bf16>(_Vector<32, __bf16>, _Vector<32, __bf16>, _Constant int)">;
4947+
def vminmaxbf16512 : X86Builtin<"_Vector<32, __bf16>(_Vector<32, __bf16>, _Vector<32, __bf16>, _Constant int)">;
49484948
}
49494949

49504950
let Features = "avx10.2-256", Attributes = [NoThrow, RequiredVectorWidth<128>] in {

‎clang/lib/Headers/avx10_2_512minmaxintrin.h‎

Lines changed: 9 additions & 9 deletions
Original file line numberDiff line numberDiff line change
@@ -14,22 +14,22 @@
1414
#ifndef __AVX10_2_512MINMAXINTRIN_H
1515
#define __AVX10_2_512MINMAXINTRIN_H
1616

17-
#define _mm512_minmaxne_pbh(A, B, C) \
18-
((__m512bh)__builtin_ia32_vminmaxnepbf16512( \
19-
(__v32bf)(__m512bh)(A), (__v32bf)(__m512bh)(A), (int)(C)))
17+
#define _mm512_minmax_pbh(A, B, C) \
18+
((__m512bh)__builtin_ia32_vminmaxbf16512((__v32bf)(__m512bh)(A), \
19+
(__v32bf)(__m512bh)(A), (int)(C)))
2020

21-
#define _mm512_mask_minmaxne_pbh(W, U, A, B, C) \
21+
#define _mm512_mask_minmax_pbh(W, U, A, B, C) \
2222
((__m512bh)__builtin_ia32_selectpbf_512( \
2323
(__mmask32)(U), \
24-
(__v32bf)_mm512_minmaxne_pbh((__v32bf)(__m512bh)(A), \
25-
(__v32bf)(__m512bh)(B), (int)(C)), \
24+
(__v32bf)_mm512_minmax_pbh((__v32bf)(__m512bh)(A), \
25+
(__v32bf)(__m512bh)(B), (int)(C)), \
2626
(__v32bf)(__m512bh)(W)))
2727

28-
#define _mm512_maskz_minmaxne_pbh(U, A, B, C) \
28+
#define _mm512_maskz_minmax_pbh(U, A, B, C) \
2929
((__m512bh)__builtin_ia32_selectpbf_512( \
3030
(__mmask32)(U), \
31-
(__v32bf)_mm512_minmaxne_pbh((__v32bf)(__m512bh)(A), \
32-
(__v32bf)(__m512bh)(B), (int)(C)), \
31+
(__v32bf)_mm512_minmax_pbh((__v32bf)(__m512bh)(A), \
32+
(__v32bf)(__m512bh)(B), (int)(C)), \
3333
(__v32bf) __builtin_bit_cast(__m512bh, _mm512_setzero_ps())))
3434

3535
#define _mm512_minmax_pd(A, B, C) \

‎clang/lib/Headers/avx10_2minmaxintrin.h‎

Lines changed: 18 additions & 18 deletions
Original file line numberDiff line numberDiff line change
@@ -14,40 +14,40 @@
1414
#ifndef __AVX10_2MINMAXINTRIN_H
1515
#define __AVX10_2MINMAXINTRIN_H
1616

17-
#define _mm_minmaxne_pbh(A, B, C) \
18-
((__m128bh)__builtin_ia32_vminmaxnepbf16128( \
19-
(__m128bh)(__v8bf)(A), (__m128bh)(__v8bf)(B), (int)(C)))
17+
#define _mm_minmax_pbh(A, B, C) \
18+
((__m128bh)__builtin_ia32_vminmaxbf16128((__m128bh)(__v8bf)(A), \
19+
(__m128bh)(__v8bf)(B), (int)(C)))
2020

21-
#define _mm_mask_minmaxne_pbh(W, U, A, B, C) \
21+
#define _mm_mask_minmax_pbh(W, U, A, B, C) \
2222
((__m128bh)__builtin_ia32_selectpbf_128( \
2323
(__mmask8)(U), \
24-
(__v8bf)_mm_minmaxne_pbh((__m128bh)(__v8bf)(A), (__m128bh)(__v8bf)(B), \
25-
(int)(C)), \
24+
(__v8bf)_mm_minmax_pbh((__m128bh)(__v8bf)(A), (__m128bh)(__v8bf)(B), \
25+
(int)(C)), \
2626
(__v8bf)(W)))
2727

28-
#define _mm_maskz_minmaxne_pbh(U, A, B, C) \
28+
#define _mm_maskz_minmax_pbh(U, A, B, C) \
2929
((__m128bh)__builtin_ia32_selectpbf_128( \
3030
(__mmask8)(U), \
31-
(__v8bf)_mm_minmaxne_pbh((__m128bh)(__v8bf)(A), (__m128bh)(__v8bf)(B), \
32-
(int)(C)), \
31+
(__v8bf)_mm_minmax_pbh((__m128bh)(__v8bf)(A), (__m128bh)(__v8bf)(B), \
32+
(int)(C)), \
3333
(__v8bf) __builtin_bit_cast(__m128bh, _mm_setzero_ps())))
3434

35-
#define _mm256_minmaxne_pbh(A, B, C) \
36-
((__m256bh)__builtin_ia32_vminmaxnepbf16256( \
37-
(__m256bh)(__v16bf)(A), (__m256bh)(__v16bf)(B), (int)(C)))
35+
#define _mm256_minmax_pbh(A, B, C) \
36+
((__m256bh)__builtin_ia32_vminmaxbf16256((__m256bh)(__v16bf)(A), \
37+
(__m256bh)(__v16bf)(B), (int)(C)))
3838

39-
#define _mm256_mask_minmaxne_pbh(W, U, A, B, C) \
39+
#define _mm256_mask_minmax_pbh(W, U, A, B, C) \
4040
((__m256bh)__builtin_ia32_selectpbf_256( \
4141
(__mmask16)(U), \
42-
(__v16bf)_mm256_minmaxne_pbh((__m256bh)(__v16bf)(A), \
43-
(__m256bh)(__v16bf)(B), (int)(C)), \
42+
(__v16bf)_mm256_minmax_pbh((__m256bh)(__v16bf)(A), \
43+
(__m256bh)(__v16bf)(B), (int)(C)), \
4444
(__v16bf)(W)))
4545

46-
#define _mm256_maskz_minmaxne_pbh(U, A, B, C) \
46+
#define _mm256_maskz_minmax_pbh(U, A, B, C) \
4747
((__m256bh)__builtin_ia32_selectpbf_256( \
4848
(__mmask16)(U), \
49-
(__v16bf)_mm256_minmaxne_pbh((__m256bh)(__v16bf)(A), \
50-
(__m256bh)(__v16bf)(B), (int)(C)), \
49+
(__v16bf)_mm256_minmax_pbh((__m256bh)(__v16bf)(A), \
50+
(__m256bh)(__v16bf)(B), (int)(C)), \
5151
(__v16bf) __builtin_bit_cast(__m256bh, _mm256_setzero_ps())))
5252

5353
#define _mm_minmax_pd(A, B, C) \

‎clang/lib/Sema/SemaX86.cpp‎

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -1045,9 +1045,9 @@ bool SemaX86::CheckBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
10451045
case X86::BI__builtin_ia32_vpshrdw128:
10461046
case X86::BI__builtin_ia32_vpshrdw256:
10471047
case X86::BI__builtin_ia32_vpshrdw512:
1048-
case X86::BI__builtin_ia32_vminmaxnepbf16128:
1049-
case X86::BI__builtin_ia32_vminmaxnepbf16256:
1050-
case X86::BI__builtin_ia32_vminmaxnepbf16512:
1048+
case X86::BI__builtin_ia32_vminmaxbf16128:
1049+
case X86::BI__builtin_ia32_vminmaxbf16256:
1050+
case X86::BI__builtin_ia32_vminmaxbf16512:
10511051
case X86::BI__builtin_ia32_vminmaxpd128_mask:
10521052
case X86::BI__builtin_ia32_vminmaxpd256_round_mask:
10531053
case X86::BI__builtin_ia32_vminmaxph128_mask:

‎clang/test/CodeGen/X86/avx10_2_512minmax-builtins.c‎

Lines changed: 12 additions & 12 deletions
Original file line numberDiff line numberDiff line change
@@ -5,25 +5,25 @@
55

66
#include <immintrin.h>
77

8-
__m512bh test_mm512_minmaxne_pbh(__m512bh __A, __m512bh __B) {
9-
// CHECK-LABEL: @test_mm512_minmaxne_pbh(
10-
// CHECK: call <32 x bfloat> @llvm.x86.avx10.vminmaxnepbf16512(
11-
return _mm512_minmaxne_pbh(__A, __B, 127);
8+
__m512bh test_mm512_minmax_pbh(__m512bh __A, __m512bh __B) {
9+
// CHECK-LABEL: @test_mm512_minmax_pbh(
10+
// CHECK: call <32 x bfloat> @llvm.x86.avx10.vminmaxbf16512(
11+
return _mm512_minmax_pbh(__A, __B, 127);
1212
}
1313

14-
__m512bh test_mm512_mask_minmaxne_pbh(__m512bh __A, __mmask32 __B, __m512bh __C, __m512bh __D) {
15-
// CHECK-LABEL: @test_mm512_mask_minmaxne_pbh(
16-
// CHECK: call <32 x bfloat> @llvm.x86.avx10.vminmaxnepbf16512(
14+
__m512bh test_mm512_mask_minmax_pbh(__m512bh __A, __mmask32 __B, __m512bh __C, __m512bh __D) {
15+
// CHECK-LABEL: @test_mm512_mask_minmax_pbh(
16+
// CHECK: call <32 x bfloat> @llvm.x86.avx10.vminmaxbf16512(
1717
// CHECK: select <32 x i1> %{{.*}}, <32 x bfloat> %{{.*}}, <32 x bfloat> %{{.*}}
18-
return _mm512_mask_minmaxne_pbh(__A, __B, __C, __D, 127);
18+
return _mm512_mask_minmax_pbh(__A, __B, __C, __D, 127);
1919
}
2020

21-
__m512bh test_mm512_maskz_minmaxne_pbh(__mmask32 __A, __m512bh __B, __m512bh __C) {
22-
// CHECK-LABEL: @test_mm512_maskz_minmaxne_pbh(
23-
// CHECK: call <32 x bfloat> @llvm.x86.avx10.vminmaxnepbf16512(
21+
__m512bh test_mm512_maskz_minmax_pbh(__mmask32 __A, __m512bh __B, __m512bh __C) {
22+
// CHECK-LABEL: @test_mm512_maskz_minmax_pbh(
23+
// CHECK: call <32 x bfloat> @llvm.x86.avx10.vminmaxbf16512(
2424
// CHECK: zeroinitializer
2525
// CHECK: select <32 x i1> %{{.*}}, <32 x bfloat> %{{.*}}, <32 x bfloat> %{{.*}}
26-
return _mm512_maskz_minmaxne_pbh(__A, __B, __C, 127);
26+
return _mm512_maskz_minmax_pbh(__A, __B, __C, 127);
2727
}
2828

2929
__m512d test_mm512_minmax_pd(__m512d __A, __m512d __B) {

‎clang/test/CodeGen/X86/avx10_2_512minmax-error.c‎

Lines changed: 12 additions & 12 deletions
Original file line numberDiff line numberDiff line change
@@ -5,20 +5,20 @@
55

66
#include <immintrin.h>
77

8-
__m128bh test_mm_minmaxne_pbh(__m128bh __A, __m128bh __B) {
9-
return _mm_minmaxne_pbh(__A, __B, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
8+
__m128bh test_mm_minmax_pbh(__m128bh __A, __m128bh __B) {
9+
return _mm_minmax_pbh(__A, __B, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
1010
}
1111

12-
__m128bh test_mm_mask_minmaxne_pbh(__m128bh __A, __mmask8 __B, __m128bh __C, __m128bh __D) {
13-
return _mm_mask_minmaxne_pbh(__A, __B, __C, __D, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
12+
__m128bh test_mm_mask_minmax_pbh(__m128bh __A, __mmask8 __B, __m128bh __C, __m128bh __D) {
13+
return _mm_mask_minmax_pbh(__A, __B, __C, __D, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
1414
}
1515

16-
__m256bh test_mm256_minmaxne_pbh(__m256bh __A, __m256bh __B) {
17-
return _mm256_minmaxne_pbh(__A, __B, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
16+
__m256bh test_mm256_minmax_pbh(__m256bh __A, __m256bh __B) {
17+
return _mm256_minmax_pbh(__A, __B, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
1818
}
1919

20-
__m256bh test_mm256_mask_minmaxne_pbh(__m256bh __A, __mmask16 __B, __m256bh __C, __m256bh __D) {
21-
return _mm256_mask_minmaxne_pbh(__A, __B, __C, __D, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
20+
__m256bh test_mm256_mask_minmax_pbh(__m256bh __A, __mmask16 __B, __m256bh __C, __m256bh __D) {
21+
return _mm256_mask_minmax_pbh(__A, __B, __C, __D, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
2222
}
2323

2424
__m128d test_mm_minmax_pd(__m128d __A, __m128d __B) {
@@ -69,12 +69,12 @@ __m256 test_mm256_mask_minmax_ps(__m256 __A, __mmask8 __B, __m256 __C, __m256 __
6969
return _mm256_mask_minmax_ps(__A, __B, __C, __D, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
7070
}
7171

72-
__m512bh test_mm512_minmaxne_pbh(__m512bh __A, __m512bh __B) {
73-
return _mm512_minmaxne_pbh(__A, __B, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
72+
__m512bh test_mm512_minmax_pbh(__m512bh __A, __m512bh __B) {
73+
return _mm512_minmax_pbh(__A, __B, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
7474
}
7575

76-
__m512bh test_mm512_mask_minmaxne_pbh(__m512bh __A, __mmask32 __B, __m512bh __C, __m512bh __D) {
77-
return _mm512_mask_minmaxne_pbh(__A, __B, __C, __D, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
76+
__m512bh test_mm512_mask_minmax_pbh(__m512bh __A, __mmask32 __B, __m512bh __C, __m512bh __D) {
77+
return _mm512_mask_minmax_pbh(__A, __B, __C, __D, 256); // expected-error {{argument value 256 is outside the valid range [0, 255]}}
7878
}
7979

8080
__m512d test_mm512_minmax_pd(__m512d __A, __m512d __B) {

‎clang/test/CodeGen/X86/avx10_2minmax-builtins.c‎

Lines changed: 24 additions & 24 deletions
Original file line numberDiff line numberDiff line change
@@ -5,46 +5,46 @@
55

66
#include <immintrin.h>
77

8-
__m128bh test_mm_minmaxne_pbh(__m128bh __A, __m128bh __B) {
9-
// CHECK-LABEL: @test_mm_minmaxne_pbh(
10-
// CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxnepbf16128(
11-
return _mm_minmaxne_pbh(__A, __B, 127);
8+
__m128bh test_mm_minmax_pbh(__m128bh __A, __m128bh __B) {
9+
// CHECK-LABEL: @test_mm_minmax_pbh(
10+
// CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxbf16128(
11+
return _mm_minmax_pbh(__A, __B, 127);
1212
}
1313

14-
__m128bh test_mm_mask_minmaxne_pbh(__m128bh __A, __mmask8 __B, __m128bh __C, __m128bh __D) {
15-
// CHECK-LABEL: @test_mm_mask_minmaxne_pbh(
16-
// CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxnepbf16128(
14+
__m128bh test_mm_mask_minmax_pbh(__m128bh __A, __mmask8 __B, __m128bh __C, __m128bh __D) {
15+
// CHECK-LABEL: @test_mm_mask_minmax_pbh(
16+
// CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxbf16128(
1717
// CHECK: select <8 x i1> %{{.*}}, <8 x bfloat> %{{.*}}, <8 x bfloat> %{{.*}}
18-
return _mm_mask_minmaxne_pbh(__A, __B, __C, __D, 127);
18+
return _mm_mask_minmax_pbh(__A, __B, __C, __D, 127);
1919
}
2020

21-
__m128bh test_mm_maskz_minmaxne_pbh(__mmask8 __A, __m128bh __B, __m128bh __C) {
22-
// CHECK-LABEL: @test_mm_maskz_minmaxne_pbh(
23-
// CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxnepbf16128(
21+
__m128bh test_mm_maskz_minmax_pbh(__mmask8 __A, __m128bh __B, __m128bh __C) {
22+
// CHECK-LABEL: @test_mm_maskz_minmax_pbh(
23+
// CHECK: call <8 x bfloat> @llvm.x86.avx10.vminmaxbf16128(
2424
// CHECK: zeroinitializer
2525
// CHECK: select <8 x i1> %{{.*}}, <8 x bfloat> %{{.*}}, <8 x bfloat> %{{.*}}
26-
return _mm_maskz_minmaxne_pbh(__A, __B, __C, 127);
26+
return _mm_maskz_minmax_pbh(__A, __B, __C, 127);
2727
}
2828

29-
__m256bh test_mm256_minmaxne_pbh(__m256bh __A, __m256bh __B) {
30-
// CHECK-LABEL: @test_mm256_minmaxne_pbh(
31-
// CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxnepbf16256(
32-
return _mm256_minmaxne_pbh(__A, __B, 127);
29+
__m256bh test_mm256_minmax_pbh(__m256bh __A, __m256bh __B) {
30+
// CHECK-LABEL: @test_mm256_minmax_pbh(
31+
// CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxbf16256(
32+
return _mm256_minmax_pbh(__A, __B, 127);
3333
}
3434

35-
__m256bh test_mm256_mask_minmaxne_pbh(__m256bh __A, __mmask16 __B, __m256bh __C, __m256bh __D) {
36-
// CHECK-LABEL: @test_mm256_mask_minmaxne_pbh(
37-
// CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxnepbf16256(
35+
__m256bh test_mm256_mask_minmax_pbh(__m256bh __A, __mmask16 __B, __m256bh __C, __m256bh __D) {
36+
// CHECK-LABEL: @test_mm256_mask_minmax_pbh(
37+
// CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxbf16256(
3838
// CHECK: select <16 x i1> %{{.*}}, <16 x bfloat> %{{.*}}, <16 x bfloat> %{{.*}}
39-
return _mm256_mask_minmaxne_pbh(__A, __B, __C, __D, 127);
39+
return _mm256_mask_minmax_pbh(__A, __B, __C, __D, 127);
4040
}
4141

42-
__m256bh test_mm256_maskz_minmaxne_pbh(__mmask16 __A, __m256bh __B, __m256bh __C) {
43-
// CHECK-LABEL: @test_mm256_maskz_minmaxne_pbh(
44-
// CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxnepbf16256(
42+
__m256bh test_mm256_maskz_minmax_pbh(__mmask16 __A, __m256bh __B, __m256bh __C) {
43+
// CHECK-LABEL: @test_mm256_maskz_minmax_pbh(
44+
// CHECK: call <16 x bfloat> @llvm.x86.avx10.vminmaxbf16256(
4545
// CHECK: zeroinitializer
4646
// CHECK: select <16 x i1> %{{.*}}, <16 x bfloat> %{{.*}}, <16 x bfloat> %{{.*}}
47-
return _mm256_maskz_minmaxne_pbh(__A, __B, __C, 127);
47+
return _mm256_maskz_minmax_pbh(__A, __B, __C, 127);
4848
}
4949

5050
__m128d test_mm_minmax_pd(__m128d __A, __m128d __B) {

‎llvm/include/llvm/IR/IntrinsicsX86.td‎

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -7279,13 +7279,13 @@ let TargetPrefix = "x86" in {
72797279
}
72807280

72817281
let TargetPrefix = "x86" in {
7282-
def int_x86_avx10_vminmaxnepbf16128 : ClangBuiltin<"__builtin_ia32_vminmaxnepbf16128">,
7282+
def int_x86_avx10_vminmaxbf16128 : ClangBuiltin<"__builtin_ia32_vminmaxbf16128">,
72837283
DefaultAttrsIntrinsic<[llvm_v8bf16_ty], [llvm_v8bf16_ty, llvm_v8bf16_ty, llvm_i32_ty],
72847284
[IntrNoMem, ImmArg<ArgIndex<2>>]>;
7285-
def int_x86_avx10_vminmaxnepbf16256 : ClangBuiltin<"__builtin_ia32_vminmaxnepbf16256">,
7285+
def int_x86_avx10_vminmaxbf16256 : ClangBuiltin<"__builtin_ia32_vminmaxbf16256">,
72867286
DefaultAttrsIntrinsic<[llvm_v16bf16_ty], [llvm_v16bf16_ty, llvm_v16bf16_ty, llvm_i32_ty],
72877287
[IntrNoMem, ImmArg<ArgIndex<2>>]>;
7288-
def int_x86_avx10_vminmaxnepbf16512 : ClangBuiltin<"__builtin_ia32_vminmaxnepbf16512">,
7288+
def int_x86_avx10_vminmaxbf16512 : ClangBuiltin<"__builtin_ia32_vminmaxbf16512">,
72897289
DefaultAttrsIntrinsic<[llvm_v32bf16_ty], [llvm_v32bf16_ty, llvm_v32bf16_ty, llvm_i32_ty],
72907290
[IntrNoMem, ImmArg<ArgIndex<2>>]>;
72917291
def int_x86_avx10_vminmaxpd128 : ClangBuiltin<"__builtin_ia32_vminmaxpd128">,

‎llvm/lib/Target/X86/X86InstrAVX10.td‎

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -447,8 +447,8 @@ multiclass avx10_minmax_scalar<string OpStr, X86VectorVTInfo _, SDNode OpNode,
447447

448448

449449
let mayRaiseFPException = 0 in
450-
defm VMINMAXNEPBF16 : avx10_minmax_packed<"vminmaxnepbf16", avx512vl_bf16_info, X86vminmax>,
451-
AVX512XDIi8Base, EVEX_CD8<16, CD8VF>, TA;
450+
defm VMINMAXBF16 : avx10_minmax_packed<"vminmaxbf16", avx512vl_bf16_info, X86vminmax>,
451+
AVX512XDIi8Base, EVEX_CD8<16, CD8VF>, TA;
452452

453453
defm VMINMAXPD : avx10_minmax_packed<"vminmaxpd", avx512vl_f64_info, X86vminmax>,
454454
avx10_minmax_packed_sae<"vminmaxpd", avx512vl_f64_info, X86vminmaxSae>,

‎llvm/lib/Target/X86/X86IntrinsicsInfo.h‎

Lines changed: 3 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -848,12 +848,9 @@ static const IntrinsicData IntrinsicsWithoutChain[] = {
848848
X86ISD::FMAX_SAE),
849849
X86_INTRINSIC_DATA(avx10_vmaxps256, INTR_TYPE_2OP_SAE, X86ISD::FMAX,
850850
X86ISD::FMAX_SAE),
851-
X86_INTRINSIC_DATA(avx10_vminmaxnepbf16128, INTR_TYPE_3OP, X86ISD::VMINMAX,
852-
0),
853-
X86_INTRINSIC_DATA(avx10_vminmaxnepbf16256, INTR_TYPE_3OP, X86ISD::VMINMAX,
854-
0),
855-
X86_INTRINSIC_DATA(avx10_vminmaxnepbf16512, INTR_TYPE_3OP, X86ISD::VMINMAX,
856-
0),
851+
X86_INTRINSIC_DATA(avx10_vminmaxbf16128, INTR_TYPE_3OP, X86ISD::VMINMAX, 0),
852+
X86_INTRINSIC_DATA(avx10_vminmaxbf16256, INTR_TYPE_3OP, X86ISD::VMINMAX, 0),
853+
X86_INTRINSIC_DATA(avx10_vminmaxbf16512, INTR_TYPE_3OP, X86ISD::VMINMAX, 0),
857854
X86_INTRINSIC_DATA(avx10_vminpd256, INTR_TYPE_2OP_SAE, X86ISD::FMIN,
858855
X86ISD::FMIN_SAE),
859856
X86_INTRINSIC_DATA(avx10_vminph256, INTR_TYPE_2OP_SAE, X86ISD::FMIN,

0 commit comments

Comments
 (0)