Skip to content

Commit da7083d

Browse files
phoebewangphoebewang
committed
[X86][AVX10.2] Remove YMM rounding from VCVT2PS2PHX (llvm#132397)
Ref: https://cdrdv2.intel.com/v1/dl/getContent/784343
1 parent 3cad497 commit da7083d

File tree

14 files changed

+13
-144
lines changed

14 files changed

+13
-144
lines changed

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

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -5009,7 +5009,7 @@ let Features = "avx10.2-256", Attributes = [NoThrow, Const, RequiredVectorWidth<
50095009
}
50105010

50115011
let Features = "avx10.2-256", Attributes = [NoThrow, Const, RequiredVectorWidth<256>] in {
5012-
def vcvt2ps2phx256_mask : X86Builtin<"_Vector<16, _Float16>(_Vector<8, float>, _Vector<8, float>, _Vector<16, _Float16>, unsigned short, _Constant int)">;
5012+
def vcvt2ps2phx256_mask : X86Builtin<"_Vector<16, _Float16>(_Vector<8, float>, _Vector<8, float>, _Vector<16, _Float16>, unsigned short)">;
50135013
}
50145014

50155015
let Features = "avx10.2-512", Attributes = [NoThrow, Const, RequiredVectorWidth<512>] in {

‎clang/lib/Headers/avx10_2convertintrin.h

Lines changed: 5 additions & 22 deletions
Original file line numberDiff line numberDiff line change
@@ -45,40 +45,23 @@ _mm_maskz_cvtx2ps_ph(__mmask8 __U, __m128 __A, __m128 __B) {
4545
static __inline__ __m256h __DEFAULT_FN_ATTRS256 _mm256_cvtx2ps_ph(__m256 __A,
4646
__m256 __B) {
4747
return (__m256h)__builtin_ia32_vcvt2ps2phx256_mask(
48-
(__v8sf)__A, (__v8sf)__B, (__v16hf)_mm256_setzero_ph(), (__mmask16)(-1),
49-
_MM_FROUND_CUR_DIRECTION);
48+
(__v8sf)__A, (__v8sf)__B, (__v16hf)_mm256_setzero_ph(), (__mmask16)(-1));
5049
}
5150

5251
static __inline__ __m256h __DEFAULT_FN_ATTRS256
5352
_mm256_mask_cvtx2ps_ph(__m256h __W, __mmask16 __U, __m256 __A, __m256 __B) {
5453
return (__m256h)__builtin_ia32_vcvt2ps2phx256_mask(
55-
(__v8sf)__A, (__v8sf)__B, (__v16hf)__W, (__mmask16)__U,
56-
_MM_FROUND_CUR_DIRECTION);
54+
(__v8sf)__A, (__v8sf)__B, (__v16hf)__W, (__mmask16)__U);
5755
}
5856

5957
static __inline__ __m256h __DEFAULT_FN_ATTRS256
6058
_mm256_maskz_cvtx2ps_ph(__mmask16 __U, __m256 __A, __m256 __B) {
6159
return (__m256h)__builtin_ia32_vcvt2ps2phx256_mask(
62-
(__v8sf)__A, (__v8sf)__B, (__v16hf)_mm256_setzero_ph(), (__mmask16)__U,
63-
_MM_FROUND_CUR_DIRECTION);
60+
(__v8sf)__A, (__v8sf)__B, (__v16hf)_mm256_setzero_ph(), (__mmask16)__U);
6461
}
6562

66-
#define _mm256_cvtx_round2ps_ph(A, B, R) \
67-
((__m256h)__builtin_ia32_vcvt2ps2phx256_mask( \
68-
(__v8sf)(A), (__v8sf)(B), (__v16hf)_mm256_undefined_ph(), \
69-
(__mmask16)(-1), (const int)(R)))
70-
71-
#define _mm256_mask_cvtx_round2ps_ph(W, U, A, B, R) \
72-
((__m256h)__builtin_ia32_vcvt2ps2phx256_mask( \
73-
(__v8sf)(A), (__v8sf)(B), (__v16hf)(W), (__mmask16)(U), (const int)(R)))
74-
75-
#define _mm256_maskz_cvtx_round2ps_ph(U, A, B, R) \
76-
((__m256h)__builtin_ia32_vcvt2ps2phx256_mask( \
77-
(__v8sf)(A), (__v8sf)(B), (__v16hf)(_mm256_setzero_ph()), \
78-
(__mmask16)(U), (const int)(R)))
79-
80-
static __inline__ __m128i __DEFAULT_FN_ATTRS128 _mm_cvtbiasph_bf8(__m128i __A,
81-
__m128h __B) {
63+
static __inline__ __m128i __DEFAULT_FN_ATTRS128
64+
_mm_cvtbiasph_bf8(__m128i __A, __m128h __B) {
8265
return (__m128i)__builtin_ia32_vcvtbiasph2bf8_128_mask(
8366
(__v16qi)__A, (__v8hf)__B, (__v16qi)_mm_undefined_si128(), (__mmask8)-1);
8467
}

‎clang/lib/Sema/SemaX86.cpp

Lines changed: 0 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -314,7 +314,6 @@ bool SemaX86::CheckBuiltinRoundingOrSAE(unsigned BuiltinID, CallExpr *TheCall) {
314314
case X86::BI__builtin_ia32_vfmulcph512_mask:
315315
case X86::BI__builtin_ia32_vfcmulcsh_mask:
316316
case X86::BI__builtin_ia32_vfcmulcph512_mask:
317-
case X86::BI__builtin_ia32_vcvt2ps2phx256_mask:
318317
case X86::BI__builtin_ia32_vcvt2ps2phx512_mask:
319318
ArgNum = 4;
320319
HasRC = true;

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

Lines changed: 0 additions & 18 deletions
Original file line numberDiff line numberDiff line change
@@ -41,24 +41,6 @@ __m256h test_mm256_maskz_cvtx2ps_ph(__mmask16 __U, __m256 __A, __m256 __B) {
4141
return _mm256_maskz_cvtx2ps_ph(__U, __A, __B);
4242
}
4343

44-
__m256h test_mm256_cvtx_round2ps_ph(__m256 __A, __m256 __B) {
45-
// CHECK-LABEL: @test_mm256_cvtx_round2ps_ph(
46-
// CHECK: call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(
47-
return _mm256_cvtx_round2ps_ph(__A, __B, _MM_FROUND_TO_ZERO | _MM_FROUND_NO_EXC);
48-
}
49-
50-
__m256h test_mm256_mask_cvtx_round2ps_ph(__m256h __W, __mmask8 __U, __m256 __A, __m256 __B) {
51-
// CHECK-LABEL: @test_mm256_mask_cvtx_round2ps_ph(
52-
// CHECK: call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(
53-
return _mm256_mask_cvtx_round2ps_ph(__W, __U, __A, __B, _MM_FROUND_TO_ZERO | _MM_FROUND_NO_EXC);
54-
}
55-
56-
__m256h test_mm256_maskz_cvtx_round2ps_ph(__mmask8 __U, __m256 __A, __m256 __B) {
57-
// CHECK-LABEL: @test_mm256_maskz_cvtx_round2ps_ph(
58-
// CHECK: call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(
59-
return _mm256_maskz_cvtx_round2ps_ph(__U, __A, __B, _MM_FROUND_TO_ZERO | _MM_FROUND_NO_EXC);
60-
}
61-
6244
__m128i test_mm_cvtbiasph_bf8(__m128i __A, __m128h __B) {
6345
// CHECK-LABEL: @test_mm_cvtbiasph_bf8(
6446
// CHECK: call <16 x i8> @llvm.x86.avx10.mask.vcvtbiasph2bf8128(

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

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -7026,8 +7026,8 @@ def int_x86_avx10_mask_vcvt2ps2phx_128 : ClangBuiltin<"__builtin_ia32_vcvt2ps2ph
70267026
DefaultAttrsIntrinsic<[llvm_v8f16_ty], [llvm_v4f32_ty, llvm_v4f32_ty, llvm_v8f16_ty, llvm_i8_ty],
70277027
[IntrNoMem]>;
70287028
def int_x86_avx10_mask_vcvt2ps2phx_256 : ClangBuiltin<"__builtin_ia32_vcvt2ps2phx256_mask">,
7029-
DefaultAttrsIntrinsic<[llvm_v16f16_ty], [llvm_v8f32_ty, llvm_v8f32_ty, llvm_v16f16_ty, llvm_i16_ty, llvm_i32_ty],
7030-
[IntrNoMem, ImmArg<ArgIndex<4>>]>;
7029+
DefaultAttrsIntrinsic<[llvm_v16f16_ty], [llvm_v8f32_ty, llvm_v8f32_ty, llvm_v16f16_ty, llvm_i16_ty],
7030+
[IntrNoMem]>;
70317031
def int_x86_avx10_mask_vcvt2ps2phx_512 : ClangBuiltin<"__builtin_ia32_vcvt2ps2phx512_mask">,
70327032
DefaultAttrsIntrinsic<[llvm_v32f16_ty], [llvm_v16f32_ty, llvm_v16f32_ty, llvm_v32f16_ty, llvm_i32_ty, llvm_i32_ty],
70337033
[IntrNoMem, ImmArg<ArgIndex<4>>]>;

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

Lines changed: 0 additions & 6 deletions
Original file line numberDiff line numberDiff line change
@@ -771,12 +771,6 @@ multiclass avx10_cvt2ps2ph<bits<8> opc, string OpcodeStr,
771771
_SrcVTInfo.info128>,
772772
EVEX_V128, EVEX_CD8<32, CD8VF>;
773773
}
774-
775-
let Predicates = [HasAVX10_2], hasEVEX_U = 1 in {
776-
defm Z256 : avx10_cvt2ps2ph_rc<opc, OpcodeStr, sched.YMM,
777-
_SrcVTInfo.info256, _DstVTInfo.info256,
778-
OpNodeRnd>;
779-
}
780774
}
781775

782776
defm VCVT2PS2PHX : avx10_cvt2ps2ph<0x67, "vcvt2ps2phx",

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

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -440,7 +440,7 @@ static const IntrinsicData IntrinsicsWithoutChain[] = {
440440
X86_INTRINSIC_DATA(avx10_mask_vcvt2ps2phx_128, INTR_TYPE_2OP_MASK,
441441
X86ISD::VFPROUND2, 0),
442442
X86_INTRINSIC_DATA(avx10_mask_vcvt2ps2phx_256, INTR_TYPE_2OP_MASK,
443-
X86ISD::VFPROUND2, X86ISD::VFPROUND2_RND),
443+
X86ISD::VFPROUND2, 0),
444444
X86_INTRINSIC_DATA(avx10_mask_vcvt2ps2phx_512, INTR_TYPE_2OP_MASK,
445445
X86ISD::VFPROUND2, X86ISD::VFPROUND2_RND),
446446
X86_INTRINSIC_DATA(avx10_mask_vcvtbiasph2bf8128, TRUNCATE2_TO_REG,

‎llvm/test/CodeGen/X86/avx10_2convert-intrinsics.ll

Lines changed: 4 additions & 45 deletions
Original file line numberDiff line numberDiff line change
@@ -50,7 +50,7 @@ define <16 x half> @test_int_x86_avx10_vcvt2ps2phx256(<8 x float> %A, <8 x float
5050
; CHECK: # %bb.0:
5151
; CHECK-NEXT: vcvt2ps2phx %ymm1, %ymm0, %ymm0 # encoding: [0x62,0xf2,0x7d,0x28,0x67,0xc1]
5252
; CHECK-NEXT: ret{{[l|q]}} # encoding: [0xc3]
53-
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> zeroinitializer, i16 -1, i32 4)
53+
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> zeroinitializer, i16 -1)
5454
ret <16 x half> %ret
5555
}
5656

@@ -66,7 +66,7 @@ define <16 x half> @test_int_x86_avx10_vcvt2ps2phx256_mask(<16 x half> %W, i16 %
6666
; X86-NEXT: kmovw {{[0-9]+}}(%esp), %k1 # encoding: [0xc5,0xf8,0x90,0x4c,0x24,0x04]
6767
; X86-NEXT: vcvt2ps2phx %ymm2, %ymm1, %ymm0 {%k1} # encoding: [0x62,0xf2,0x75,0x29,0x67,0xc2]
6868
; X86-NEXT: retl # encoding: [0xc3]
69-
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> %W, i16 %U, i32 4)
69+
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> %W, i16 %U)
7070
ret <16 x half> %ret
7171
}
7272

@@ -82,52 +82,11 @@ define <16 x half> @test_int_x86_avx10_vcvt2ps2phx256_maskz(<16 x half> %W, i16
8282
; X86-NEXT: kmovw {{[0-9]+}}(%esp), %k1 # encoding: [0xc5,0xf8,0x90,0x4c,0x24,0x04]
8383
; X86-NEXT: vcvt2ps2phx %ymm2, %ymm1, %ymm0 {%k1} {z} # encoding: [0x62,0xf2,0x75,0xa9,0x67,0xc2]
8484
; X86-NEXT: retl # encoding: [0xc3]
85-
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> zeroinitializer, i16 %U, i32 4)
85+
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> zeroinitializer, i16 %U)
8686
ret <16 x half> %ret
8787
}
8888

89-
define <16 x half> @test_int_x86_avx10_vcvt2ps2phx256_round(<8 x float> %A, <8 x float> %B) {
90-
; CHECK-LABEL: test_int_x86_avx10_vcvt2ps2phx256_round:
91-
; CHECK: # %bb.0:
92-
; CHECK-NEXT: vcvt2ps2phx {rz-sae}, %ymm1, %ymm0, %ymm0 # encoding: [0x62,0xf2,0x79,0x78,0x67,0xc1]
93-
; CHECK-NEXT: ret{{[l|q]}} # encoding: [0xc3]
94-
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> zeroinitializer, i16 -1, i32 11)
95-
ret <16 x half> %ret
96-
}
97-
98-
define <16 x half> @test_int_x86_avx10_vcvt2ps2phx256_round_mask(<16 x half> %W, i16 %U, <8 x float> %A, <8 x float> %B) {
99-
; X64-LABEL: test_int_x86_avx10_vcvt2ps2phx256_round_mask:
100-
; X64: # %bb.0:
101-
; X64-NEXT: kmovd %edi, %k1 # encoding: [0xc5,0xfb,0x92,0xcf]
102-
; X64-NEXT: vcvt2ps2phx {rz-sae}, %ymm2, %ymm1, %ymm0 {%k1} # encoding: [0x62,0xf2,0x71,0x79,0x67,0xc2]
103-
; X64-NEXT: retq # encoding: [0xc3]
104-
;
105-
; X86-LABEL: test_int_x86_avx10_vcvt2ps2phx256_round_mask:
106-
; X86: # %bb.0:
107-
; X86-NEXT: kmovw {{[0-9]+}}(%esp), %k1 # encoding: [0xc5,0xf8,0x90,0x4c,0x24,0x04]
108-
; X86-NEXT: vcvt2ps2phx {rz-sae}, %ymm2, %ymm1, %ymm0 {%k1} # encoding: [0x62,0xf2,0x71,0x79,0x67,0xc2]
109-
; X86-NEXT: retl # encoding: [0xc3]
110-
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> %W, i16 %U, i32 11)
111-
ret <16 x half> %ret
112-
}
113-
114-
define <16 x half> @test_int_x86_avx10_vcvt2ps2phx256_round_maskz(i16 %U, <8 x float> %A, <8 x float> %B) {
115-
; X64-LABEL: test_int_x86_avx10_vcvt2ps2phx256_round_maskz:
116-
; X64: # %bb.0:
117-
; X64-NEXT: kmovd %edi, %k1 # encoding: [0xc5,0xfb,0x92,0xcf]
118-
; X64-NEXT: vcvt2ps2phx {rz-sae}, %ymm1, %ymm0, %ymm0 {%k1} {z} # encoding: [0x62,0xf2,0x79,0xf9,0x67,0xc1]
119-
; X64-NEXT: retq # encoding: [0xc3]
120-
;
121-
; X86-LABEL: test_int_x86_avx10_vcvt2ps2phx256_round_maskz:
122-
; X86: # %bb.0:
123-
; X86-NEXT: kmovw {{[0-9]+}}(%esp), %k1 # encoding: [0xc5,0xf8,0x90,0x4c,0x24,0x04]
124-
; X86-NEXT: vcvt2ps2phx {rz-sae}, %ymm1, %ymm0, %ymm0 {%k1} {z} # encoding: [0x62,0xf2,0x79,0xf9,0x67,0xc1]
125-
; X86-NEXT: retl # encoding: [0xc3]
126-
%ret = call <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float> %A, <8 x float> %B, <16 x half> zeroinitializer, i16 %U, i32 11)
127-
ret <16 x half> %ret
128-
}
129-
130-
declare <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float>, <8 x float>, <16 x half>, i16, i32)
89+
declare <16 x half> @llvm.x86.avx10.mask.vcvt2ps2phx.256(<8 x float>, <8 x float>, <16 x half>, i16)
13190

13291
define <16 x i8> @test_int_x86_avx10_vcvtbiasph2bf8128(<16 x i8> %A, <8 x half> %B) nounwind {
13392
; CHECK-LABEL: test_int_x86_avx10_vcvtbiasph2bf8128:

‎llvm/test/MC/Disassembler/X86/avx10.2convert-32.txt

Lines changed: 0 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -5,18 +5,10 @@
55
# INTEL: vcvt2ps2phx ymm2, ymm3, ymm4
66
0x62,0xf2,0x65,0x28,0x67,0xd4
77

8-
# ATT: vcvt2ps2phx {rn-sae}, %ymm4, %ymm3, %ymm2
9-
# INTEL: vcvt2ps2phx ymm2, ymm3, ymm4, {rn-sae}
10-
0x62,0xf2,0x61,0x18,0x67,0xd4
11-
128
# ATT: vcvt2ps2phx %ymm4, %ymm3, %ymm2 {%k7}
139
# INTEL: vcvt2ps2phx ymm2 {k7}, ymm3, ymm4
1410
0x62,0xf2,0x65,0x2f,0x67,0xd4
1511

16-
# ATT: vcvt2ps2phx {rz-sae}, %ymm4, %ymm3, %ymm2 {%k7} {z}
17-
# INTEL: vcvt2ps2phx ymm2 {k7} {z}, ymm3, ymm4, {rz-sae}
18-
0x62,0xf2,0x61,0xff,0x67,0xd4
19-
2012
# ATT: vcvt2ps2phx %zmm4, %zmm3, %zmm2
2113
# INTEL: vcvt2ps2phx zmm2, zmm3, zmm4
2214
0x62,0xf2,0x65,0x48,0x67,0xd4

‎llvm/test/MC/Disassembler/X86/avx10.2convert-64.txt

Lines changed: 0 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -5,18 +5,10 @@
55
# INTEL: vcvt2ps2phx ymm22, ymm23, ymm24
66
0x62,0x82,0x45,0x20,0x67,0xf0
77

8-
# ATT: vcvt2ps2phx {rn-sae}, %ymm24, %ymm23, %ymm22
9-
# INTEL: vcvt2ps2phx ymm22, ymm23, ymm24, {rn-sae}
10-
0x62,0x82,0x41,0x10,0x67,0xf0
11-
128
# ATT: vcvt2ps2phx %ymm24, %ymm23, %ymm22 {%k7}
139
# INTEL: vcvt2ps2phx ymm22 {k7}, ymm23, ymm24
1410
0x62,0x82,0x45,0x27,0x67,0xf0
1511

16-
# ATT: vcvt2ps2phx {rz-sae}, %ymm24, %ymm23, %ymm22 {%k7} {z}
17-
# INTEL: vcvt2ps2phx ymm22 {k7} {z}, ymm23, ymm24, {rz-sae}
18-
0x62,0x82,0x41,0xf7,0x67,0xf0
19-
2012
# ATT: vcvt2ps2phx %zmm24, %zmm23, %zmm22
2113
# INTEL: vcvt2ps2phx zmm22, zmm23, zmm24
2214
0x62,0x82,0x45,0x40,0x67,0xf0

‎llvm/test/MC/X86/avx10.2convert-32-att.s

Lines changed: 0 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -4,18 +4,10 @@
44
// CHECK: encoding: [0x62,0xf2,0x65,0x28,0x67,0xd4]
55
vcvt2ps2phx %ymm4, %ymm3, %ymm2
66

7-
// CHECK: vcvt2ps2phx {rn-sae}, %ymm4, %ymm3, %ymm2
8-
// CHECK: encoding: [0x62,0xf2,0x61,0x18,0x67,0xd4]
9-
vcvt2ps2phx {rn-sae}, %ymm4, %ymm3, %ymm2
10-
117
// CHECK: vcvt2ps2phx %ymm4, %ymm3, %ymm2 {%k7}
128
// CHECK: encoding: [0x62,0xf2,0x65,0x2f,0x67,0xd4]
139
vcvt2ps2phx %ymm4, %ymm3, %ymm2 {%k7}
1410

15-
// CHECK: vcvt2ps2phx {rz-sae}, %ymm4, %ymm3, %ymm2 {%k7} {z}
16-
// CHECK: encoding: [0x62,0xf2,0x61,0xff,0x67,0xd4]
17-
vcvt2ps2phx {rz-sae}, %ymm4, %ymm3, %ymm2 {%k7} {z}
18-
1911
// CHECK: vcvt2ps2phx %zmm4, %zmm3, %zmm2
2012
// CHECK: encoding: [0x62,0xf2,0x65,0x48,0x67,0xd4]
2113
vcvt2ps2phx %zmm4, %zmm3, %zmm2

‎llvm/test/MC/X86/avx10.2convert-32-intel.s

Lines changed: 0 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -4,18 +4,10 @@
44
// CHECK: encoding: [0x62,0xf2,0x65,0x28,0x67,0xd4]
55
vcvt2ps2phx ymm2, ymm3, ymm4
66

7-
// CHECK: vcvt2ps2phx ymm2, ymm3, ymm4, {rn-sae}
8-
// CHECK: encoding: [0x62,0xf2,0x61,0x18,0x67,0xd4]
9-
vcvt2ps2phx ymm2, ymm3, ymm4, {rn-sae}
10-
117
// CHECK: vcvt2ps2phx ymm2 {k7}, ymm3, ymm4
128
// CHECK: encoding: [0x62,0xf2,0x65,0x2f,0x67,0xd4]
139
vcvt2ps2phx ymm2 {k7}, ymm3, ymm4
1410

15-
// CHECK: vcvt2ps2phx ymm2 {k7} {z}, ymm3, ymm4, {rz-sae}
16-
// CHECK: encoding: [0x62,0xf2,0x61,0xff,0x67,0xd4]
17-
vcvt2ps2phx ymm2 {k7} {z}, ymm3, ymm4, {rz-sae}
18-
1911
// CHECK: vcvt2ps2phx zmm2, zmm3, zmm4
2012
// CHECK: encoding: [0x62,0xf2,0x65,0x48,0x67,0xd4]
2113
vcvt2ps2phx zmm2, zmm3, zmm4

‎llvm/test/MC/X86/avx10.2convert-64-att.s

Lines changed: 0 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -4,18 +4,10 @@
44
// CHECK: encoding: [0x62,0x82,0x45,0x20,0x67,0xf0]
55
vcvt2ps2phx %ymm24, %ymm23, %ymm22
66

7-
// CHECK: vcvt2ps2phx {rn-sae}, %ymm24, %ymm23, %ymm22
8-
// CHECK: encoding: [0x62,0x82,0x41,0x10,0x67,0xf0]
9-
vcvt2ps2phx {rn-sae}, %ymm24, %ymm23, %ymm22
10-
117
// CHECK: vcvt2ps2phx %ymm24, %ymm23, %ymm22 {%k7}
128
// CHECK: encoding: [0x62,0x82,0x45,0x27,0x67,0xf0]
139
vcvt2ps2phx %ymm24, %ymm23, %ymm22 {%k7}
1410

15-
// CHECK: vcvt2ps2phx {rz-sae}, %ymm24, %ymm23, %ymm22 {%k7} {z}
16-
// CHECK: encoding: [0x62,0x82,0x41,0xf7,0x67,0xf0]
17-
vcvt2ps2phx {rz-sae}, %ymm24, %ymm23, %ymm22 {%k7} {z}
18-
1911
// CHECK: vcvt2ps2phx %zmm24, %zmm23, %zmm22
2012
// CHECK: encoding: [0x62,0x82,0x45,0x40,0x67,0xf0]
2113
vcvt2ps2phx %zmm24, %zmm23, %zmm22

‎llvm/test/MC/X86/avx10.2convert-64-intel.s

Lines changed: 0 additions & 8 deletions
Original file line numberDiff line numberDiff line change
@@ -4,18 +4,10 @@
44
// CHECK: encoding: [0x62,0x82,0x45,0x20,0x67,0xf0]
55
vcvt2ps2phx ymm22, ymm23, ymm24
66

7-
// CHECK: vcvt2ps2phx ymm22, ymm23, ymm24, {rn-sae}
8-
// CHECK: encoding: [0x62,0x82,0x41,0x10,0x67,0xf0]
9-
vcvt2ps2phx ymm22, ymm23, ymm24, {rn-sae}
10-
117
// CHECK: vcvt2ps2phx ymm22 {k7}, ymm23, ymm24
128
// CHECK: encoding: [0x62,0x82,0x45,0x27,0x67,0xf0]
139
vcvt2ps2phx ymm22 {k7}, ymm23, ymm24
1410

15-
// CHECK: vcvt2ps2phx ymm22 {k7} {z}, ymm23, ymm24, {rz-sae}
16-
// CHECK: encoding: [0x62,0x82,0x41,0xf7,0x67,0xf0]
17-
vcvt2ps2phx ymm22 {k7} {z}, ymm23, ymm24, {rz-sae}
18-
1911
// CHECK: vcvt2ps2phx zmm22, zmm23, zmm24
2012
// CHECK: encoding: [0x62,0x82,0x45,0x40,0x67,0xf0]
2113
vcvt2ps2phx zmm22, zmm23, zmm24

0 commit comments

Comments
 (0)