Skip to content

Commit 840809c

Browse files
SC llvm teamSC llvm team
SC llvm team
authored and
SC llvm team
committed
Merged main:48fcfaf2ba51 into amd-gfx:e99bfc56fcd4
Local branch amd-gfx e99bfc5 Merged main:a991ccd8efec into amd-gfx:b7ec5b5aa5db Remote branch main 48fcfaf [NFC][mlir][bufferization] Add paragraph about runtime and space cost to bufferization.dealloc op documentation (llvm#65612)
2 parents e99bfc5 + 48fcfaf commit 840809c

File tree

93 files changed

+6475
-1237
lines changed

Some content is hidden

Large Commits have some content hidden by default. Use the searchbox below for content that may be hidden.

93 files changed

+6475
-1237
lines changed

‎clang/docs/ReleaseNotes.rst

Lines changed: 0 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -302,9 +302,6 @@ AMDGPU Support
302302
X86 Support
303303
^^^^^^^^^^^
304304

305-
- Added option ``-m[no-]evex512`` to disable ZMM and 64-bit mask instructions
306-
for AVX512 features.
307-
308305
Arm and AArch64 Support
309306
^^^^^^^^^^^^^^^^^^^^^^^
310307

‎clang/include/clang/Basic/BuiltinsX86.def

Lines changed: 441 additions & 441 deletions
Large diffs are not rendered by default.

‎clang/include/clang/Driver/Options.td

Lines changed: 0 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -5744,8 +5744,6 @@ def mcx16 : Flag<["-"], "mcx16">, Group<m_x86_Features_Group>;
57445744
def mno_cx16 : Flag<["-"], "mno-cx16">, Group<m_x86_Features_Group>;
57455745
def menqcmd : Flag<["-"], "menqcmd">, Group<m_x86_Features_Group>;
57465746
def mno_enqcmd : Flag<["-"], "mno-enqcmd">, Group<m_x86_Features_Group>;
5747-
def mevex512 : Flag<["-"], "mevex512">, Group<m_x86_Features_Group>;
5748-
def mno_evex512 : Flag<["-"], "mno-evex512">, Group<m_x86_Features_Group>;
57495747
def mf16c : Flag<["-"], "mf16c">, Group<m_x86_Features_Group>;
57505748
def mno_f16c : Flag<["-"], "mno-f16c">, Group<m_x86_Features_Group>;
57515749
def mfma : Flag<["-"], "mfma">, Group<m_x86_Features_Group>;

‎clang/lib/Basic/Targets/X86.cpp

Lines changed: 4 additions & 24 deletions
Original file line numberDiff line numberDiff line change
@@ -119,8 +119,6 @@ bool X86TargetInfo::initFeatureMap(
119119
setFeatureEnabled(Features, F, true);
120120

121121
std::vector<std::string> UpdatedFeaturesVec;
122-
bool HasEVEX512 = true;
123-
bool HasAVX512F = false;
124122
for (const auto &Feature : FeaturesVec) {
125123
// Expand general-regs-only to -x86, -mmx and -sse
126124
if (Feature == "+general-regs-only") {
@@ -130,17 +128,8 @@ bool X86TargetInfo::initFeatureMap(
130128
continue;
131129
}
132130

133-
if (!HasAVX512F && Feature.substr(0, 7) == "+avx512")
134-
HasAVX512F = true;
135-
if (HasAVX512F && Feature == "-avx512f")
136-
HasAVX512F = false;
137-
if (HasEVEX512 && Feature == "-evex512")
138-
HasEVEX512 = false;
139-
140131
UpdatedFeaturesVec.push_back(Feature);
141132
}
142-
if (HasAVX512F && HasEVEX512)
143-
UpdatedFeaturesVec.push_back("+evex512");
144133

145134
if (!TargetInfo::initFeatureMap(Features, Diags, CPU, UpdatedFeaturesVec))
146135
return false;
@@ -239,8 +228,6 @@ bool X86TargetInfo::handleTargetFeatures(std::vector<std::string> &Features,
239228
HasF16C = true;
240229
} else if (Feature == "+gfni") {
241230
HasGFNI = true;
242-
} else if (Feature == "+evex512") {
243-
HasEVEX512 = true;
244231
} else if (Feature == "+avx512cd") {
245232
HasAVX512CD = true;
246233
} else if (Feature == "+avx512vpopcntdq") {
@@ -744,8 +731,6 @@ void X86TargetInfo::getTargetDefines(const LangOptions &Opts,
744731
if (HasGFNI)
745732
Builder.defineMacro("__GFNI__");
746733

747-
if (HasEVEX512)
748-
Builder.defineMacro("__EVEX512__");
749734
if (HasAVX512CD)
750735
Builder.defineMacro("__AVX512CD__");
751736
if (HasAVX512VPOPCNTDQ)
@@ -1001,7 +986,6 @@ bool X86TargetInfo::isValidFeatureName(StringRef Name) const {
1001986
.Case("crc32", true)
1002987
.Case("cx16", true)
1003988
.Case("enqcmd", true)
1004-
.Case("evex512", true)
1005989
.Case("f16c", true)
1006990
.Case("fma", true)
1007991
.Case("fma4", true)
@@ -1109,7 +1093,6 @@ bool X86TargetInfo::hasFeature(StringRef Feature) const {
11091093
.Case("cx8", HasCX8)
11101094
.Case("cx16", HasCX16)
11111095
.Case("enqcmd", HasENQCMD)
1112-
.Case("evex512", HasEVEX512)
11131096
.Case("f16c", HasF16C)
11141097
.Case("fma", HasFMA)
11151098
.Case("fma4", XOPLevel >= FMA4)
@@ -1550,9 +1533,8 @@ bool X86TargetInfo::validateOperandSize(const llvm::StringMap<bool> &FeatureMap,
15501533
return Size <= 64;
15511534
case 'z':
15521535
// XMM0/YMM/ZMM0
1553-
if (hasFeatureEnabled(FeatureMap, "avx512f") &&
1554-
hasFeatureEnabled(FeatureMap, "evex512"))
1555-
// ZMM0 can be used if target supports AVX512F and EVEX512 is set.
1536+
if (hasFeatureEnabled(FeatureMap, "avx512f"))
1537+
// ZMM0 can be used if target supports AVX512F.
15561538
return Size <= 512U;
15571539
else if (hasFeatureEnabled(FeatureMap, "avx"))
15581540
// YMM0 can be used if target supports AVX.
@@ -1571,10 +1553,8 @@ bool X86TargetInfo::validateOperandSize(const llvm::StringMap<bool> &FeatureMap,
15711553
break;
15721554
case 'v':
15731555
case 'x':
1574-
if (hasFeatureEnabled(FeatureMap, "avx512f") &&
1575-
hasFeatureEnabled(FeatureMap, "evex512"))
1576-
// 512-bit zmm registers can be used if target supports AVX512F and
1577-
// EVEX512 is set.
1556+
if (hasFeatureEnabled(FeatureMap, "avx512f"))
1557+
// 512-bit zmm registers can be used if target supports AVX512F.
15781558
return Size <= 512U;
15791559
else if (hasFeatureEnabled(FeatureMap, "avx"))
15801560
// 256-bit ymm registers can be used if target supports AVX.

‎clang/lib/Basic/Targets/X86.h

Lines changed: 0 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -95,7 +95,6 @@ class LLVM_LIBRARY_VISIBILITY X86TargetInfo : public TargetInfo {
9595
bool HasLWP = false;
9696
bool HasFMA = false;
9797
bool HasF16C = false;
98-
bool HasEVEX512 = false;
9998
bool HasAVX512CD = false;
10099
bool HasAVX512VPOPCNTDQ = false;
101100
bool HasAVX512VNNI = false;

‎clang/lib/CodeGen/Targets/X86.cpp

Lines changed: 2 additions & 20 deletions
Original file line numberDiff line numberDiff line change
@@ -1508,33 +1508,15 @@ static bool checkAVXParamFeature(DiagnosticsEngine &Diag,
15081508
return false;
15091509
}
15101510

1511-
static bool checkAVX512ParamFeature(DiagnosticsEngine &Diag,
1512-
SourceLocation CallLoc,
1513-
const llvm::StringMap<bool> &CallerMap,
1514-
const llvm::StringMap<bool> &CalleeMap,
1515-
QualType Ty, bool IsArgument) {
1516-
bool Caller256 = CallerMap.lookup("avx512f") && !CallerMap.lookup("evex512");
1517-
bool Callee256 = CalleeMap.lookup("avx512f") && !CalleeMap.lookup("evex512");
1518-
1519-
// Forbid 512-bit or larger vector pass or return when we disabled ZMM
1520-
// instructions.
1521-
if (Caller256 || Callee256)
1522-
return Diag.Report(CallLoc, diag::err_avx_calling_convention)
1523-
<< IsArgument << Ty << "evex512";
1524-
1525-
return checkAVXParamFeature(Diag, CallLoc, CallerMap, CalleeMap, Ty,
1526-
"avx512f", IsArgument);
1527-
}
1528-
15291511
static bool checkAVXParam(DiagnosticsEngine &Diag, ASTContext &Ctx,
15301512
SourceLocation CallLoc,
15311513
const llvm::StringMap<bool> &CallerMap,
15321514
const llvm::StringMap<bool> &CalleeMap, QualType Ty,
15331515
bool IsArgument) {
15341516
uint64_t Size = Ctx.getTypeSize(Ty);
15351517
if (Size > 256)
1536-
return checkAVX512ParamFeature(Diag, CallLoc, CallerMap, CalleeMap, Ty,
1537-
IsArgument);
1518+
return checkAVXParamFeature(Diag, CallLoc, CallerMap, CalleeMap, Ty,
1519+
"avx512f", IsArgument);
15381520

15391521
if (Size > 128)
15401522
return checkAVXParamFeature(Diag, CallLoc, CallerMap, CalleeMap, Ty, "avx",

‎clang/lib/Headers/avx512bf16intrin.h

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -20,7 +20,7 @@ typedef __bf16 __m512bh __attribute__((__vector_size__(64), __aligned__(64)));
2020
typedef __bf16 __bfloat16 __attribute__((deprecated("use __bf16 instead")));
2121

2222
#define __DEFAULT_FN_ATTRS512 \
23-
__attribute__((__always_inline__, __nodebug__, __target__("avx512bf16,evex512"), \
23+
__attribute__((__always_inline__, __nodebug__, __target__("avx512bf16"), \
2424
__min_vector_width__(512)))
2525
#define __DEFAULT_FN_ATTRS \
2626
__attribute__((__always_inline__, __nodebug__, __target__("avx512bf16")))

‎clang/lib/Headers/avx512bitalgintrin.h

Lines changed: 1 addition & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -15,10 +15,7 @@
1515
#define __AVX512BITALGINTRIN_H
1616

1717
/* Define the default attributes for the functions in this file. */
18-
#define __DEFAULT_FN_ATTRS \
19-
__attribute__((__always_inline__, __nodebug__, \
20-
__target__("avx512bitalg,evex512"), \
21-
__min_vector_width__(512)))
18+
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512bitalg"), __min_vector_width__(512)))
2219

2320
static __inline__ __m512i __DEFAULT_FN_ATTRS
2421
_mm512_popcnt_epi16(__m512i __A)

‎clang/lib/Headers/avx512bwintrin.h

Lines changed: 19 additions & 20 deletions
Original file line numberDiff line numberDiff line change
@@ -18,8 +18,7 @@ typedef unsigned int __mmask32;
1818
typedef unsigned long long __mmask64;
1919

2020
/* Define the default attributes for the functions in this file. */
21-
#define __DEFAULT_FN_ATTRS512 __attribute__((__always_inline__, __nodebug__, __target__("avx512bw,evex512"), __min_vector_width__(512)))
22-
#define __DEFAULT_FN_ATTRS64 __attribute__((__always_inline__, __nodebug__, __target__("avx512bw,evex512")))
21+
#define __DEFAULT_FN_ATTRS512 __attribute__((__always_inline__, __nodebug__, __target__("avx512bw"), __min_vector_width__(512)))
2322
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512bw")))
2423

2524
static __inline __mmask32 __DEFAULT_FN_ATTRS
@@ -28,7 +27,7 @@ _knot_mask32(__mmask32 __M)
2827
return __builtin_ia32_knotsi(__M);
2928
}
3029

31-
static __inline __mmask64 __DEFAULT_FN_ATTRS64
30+
static __inline __mmask64 __DEFAULT_FN_ATTRS
3231
_knot_mask64(__mmask64 __M)
3332
{
3433
return __builtin_ia32_knotdi(__M);
@@ -40,7 +39,7 @@ _kand_mask32(__mmask32 __A, __mmask32 __B)
4039
return (__mmask32)__builtin_ia32_kandsi((__mmask32)__A, (__mmask32)__B);
4140
}
4241

43-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
42+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
4443
_kand_mask64(__mmask64 __A, __mmask64 __B)
4544
{
4645
return (__mmask64)__builtin_ia32_kanddi((__mmask64)__A, (__mmask64)__B);
@@ -52,7 +51,7 @@ _kandn_mask32(__mmask32 __A, __mmask32 __B)
5251
return (__mmask32)__builtin_ia32_kandnsi((__mmask32)__A, (__mmask32)__B);
5352
}
5453

55-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
54+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
5655
_kandn_mask64(__mmask64 __A, __mmask64 __B)
5756
{
5857
return (__mmask64)__builtin_ia32_kandndi((__mmask64)__A, (__mmask64)__B);
@@ -64,7 +63,7 @@ _kor_mask32(__mmask32 __A, __mmask32 __B)
6463
return (__mmask32)__builtin_ia32_korsi((__mmask32)__A, (__mmask32)__B);
6564
}
6665

67-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
66+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
6867
_kor_mask64(__mmask64 __A, __mmask64 __B)
6968
{
7069
return (__mmask64)__builtin_ia32_kordi((__mmask64)__A, (__mmask64)__B);
@@ -76,7 +75,7 @@ _kxnor_mask32(__mmask32 __A, __mmask32 __B)
7675
return (__mmask32)__builtin_ia32_kxnorsi((__mmask32)__A, (__mmask32)__B);
7776
}
7877

79-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
78+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
8079
_kxnor_mask64(__mmask64 __A, __mmask64 __B)
8180
{
8281
return (__mmask64)__builtin_ia32_kxnordi((__mmask64)__A, (__mmask64)__B);
@@ -88,7 +87,7 @@ _kxor_mask32(__mmask32 __A, __mmask32 __B)
8887
return (__mmask32)__builtin_ia32_kxorsi((__mmask32)__A, (__mmask32)__B);
8988
}
9089

91-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
90+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
9291
_kxor_mask64(__mmask64 __A, __mmask64 __B)
9392
{
9493
return (__mmask64)__builtin_ia32_kxordi((__mmask64)__A, (__mmask64)__B);
@@ -112,19 +111,19 @@ _kortest_mask32_u8(__mmask32 __A, __mmask32 __B, unsigned char *__C) {
112111
return (unsigned char)__builtin_ia32_kortestzsi(__A, __B);
113112
}
114113

115-
static __inline__ unsigned char __DEFAULT_FN_ATTRS64
114+
static __inline__ unsigned char __DEFAULT_FN_ATTRS
116115
_kortestc_mask64_u8(__mmask64 __A, __mmask64 __B)
117116
{
118117
return (unsigned char)__builtin_ia32_kortestcdi(__A, __B);
119118
}
120119

121-
static __inline__ unsigned char __DEFAULT_FN_ATTRS64
120+
static __inline__ unsigned char __DEFAULT_FN_ATTRS
122121
_kortestz_mask64_u8(__mmask64 __A, __mmask64 __B)
123122
{
124123
return (unsigned char)__builtin_ia32_kortestzdi(__A, __B);
125124
}
126125

127-
static __inline__ unsigned char __DEFAULT_FN_ATTRS64
126+
static __inline__ unsigned char __DEFAULT_FN_ATTRS
128127
_kortest_mask64_u8(__mmask64 __A, __mmask64 __B, unsigned char *__C) {
129128
*__C = (unsigned char)__builtin_ia32_kortestcdi(__A, __B);
130129
return (unsigned char)__builtin_ia32_kortestzdi(__A, __B);
@@ -148,19 +147,19 @@ _ktest_mask32_u8(__mmask32 __A, __mmask32 __B, unsigned char *__C) {
148147
return (unsigned char)__builtin_ia32_ktestzsi(__A, __B);
149148
}
150149

151-
static __inline__ unsigned char __DEFAULT_FN_ATTRS64
150+
static __inline__ unsigned char __DEFAULT_FN_ATTRS
152151
_ktestc_mask64_u8(__mmask64 __A, __mmask64 __B)
153152
{
154153
return (unsigned char)__builtin_ia32_ktestcdi(__A, __B);
155154
}
156155

157-
static __inline__ unsigned char __DEFAULT_FN_ATTRS64
156+
static __inline__ unsigned char __DEFAULT_FN_ATTRS
158157
_ktestz_mask64_u8(__mmask64 __A, __mmask64 __B)
159158
{
160159
return (unsigned char)__builtin_ia32_ktestzdi(__A, __B);
161160
}
162161

163-
static __inline__ unsigned char __DEFAULT_FN_ATTRS64
162+
static __inline__ unsigned char __DEFAULT_FN_ATTRS
164163
_ktest_mask64_u8(__mmask64 __A, __mmask64 __B, unsigned char *__C) {
165164
*__C = (unsigned char)__builtin_ia32_ktestcdi(__A, __B);
166165
return (unsigned char)__builtin_ia32_ktestzdi(__A, __B);
@@ -172,7 +171,7 @@ _kadd_mask32(__mmask32 __A, __mmask32 __B)
172171
return (__mmask32)__builtin_ia32_kaddsi((__mmask32)__A, (__mmask32)__B);
173172
}
174173

175-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
174+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
176175
_kadd_mask64(__mmask64 __A, __mmask64 __B)
177176
{
178177
return (__mmask64)__builtin_ia32_kadddi((__mmask64)__A, (__mmask64)__B);
@@ -195,7 +194,7 @@ _cvtmask32_u32(__mmask32 __A) {
195194
return (unsigned int)__builtin_ia32_kmovd((__mmask32)__A);
196195
}
197196

198-
static __inline__ unsigned long long __DEFAULT_FN_ATTRS64
197+
static __inline__ unsigned long long __DEFAULT_FN_ATTRS
199198
_cvtmask64_u64(__mmask64 __A) {
200199
return (unsigned long long)__builtin_ia32_kmovq((__mmask64)__A);
201200
}
@@ -205,7 +204,7 @@ _cvtu32_mask32(unsigned int __A) {
205204
return (__mmask32)__builtin_ia32_kmovd((__mmask32)__A);
206205
}
207206

208-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
207+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
209208
_cvtu64_mask64(unsigned long long __A) {
210209
return (__mmask64)__builtin_ia32_kmovq((__mmask64)__A);
211210
}
@@ -215,7 +214,7 @@ _load_mask32(__mmask32 *__A) {
215214
return (__mmask32)__builtin_ia32_kmovd(*(__mmask32 *)__A);
216215
}
217216

218-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
217+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
219218
_load_mask64(__mmask64 *__A) {
220219
return (__mmask64)__builtin_ia32_kmovq(*(__mmask64 *)__A);
221220
}
@@ -225,7 +224,7 @@ _store_mask32(__mmask32 *__A, __mmask32 __B) {
225224
*(__mmask32 *)__A = __builtin_ia32_kmovd((__mmask32)__B);
226225
}
227226

228-
static __inline__ void __DEFAULT_FN_ATTRS64
227+
static __inline__ void __DEFAULT_FN_ATTRS
229228
_store_mask64(__mmask64 *__A, __mmask64 __B) {
230229
*(__mmask64 *)__A = __builtin_ia32_kmovq((__mmask64)__B);
231230
}
@@ -1715,7 +1714,7 @@ _mm512_maskz_set1_epi8 (__mmask64 __M, char __A)
17151714
(__v64qi) _mm512_setzero_si512());
17161715
}
17171716

1718-
static __inline__ __mmask64 __DEFAULT_FN_ATTRS64
1717+
static __inline__ __mmask64 __DEFAULT_FN_ATTRS
17191718
_mm512_kunpackd (__mmask64 __A, __mmask64 __B)
17201719
{
17211720
return (__mmask64) __builtin_ia32_kunpckdi ((__mmask64) __A,

‎clang/lib/Headers/avx512cdintrin.h

Lines changed: 1 addition & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -15,9 +15,7 @@
1515
#define __AVX512CDINTRIN_H
1616

1717
/* Define the default attributes for the functions in this file. */
18-
#define __DEFAULT_FN_ATTRS \
19-
__attribute__((__always_inline__, __nodebug__, \
20-
__target__("avx512cd,evex512"), __min_vector_width__(512)))
18+
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512cd"), __min_vector_width__(512)))
2119

2220
static __inline__ __m512i __DEFAULT_FN_ATTRS
2321
_mm512_conflict_epi64 (__m512i __A)

‎clang/lib/Headers/avx512dqintrin.h

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -15,7 +15,7 @@
1515
#define __AVX512DQINTRIN_H
1616

1717
/* Define the default attributes for the functions in this file. */
18-
#define __DEFAULT_FN_ATTRS512 __attribute__((__always_inline__, __nodebug__, __target__("avx512dq,evex512"), __min_vector_width__(512)))
18+
#define __DEFAULT_FN_ATTRS512 __attribute__((__always_inline__, __nodebug__, __target__("avx512dq"), __min_vector_width__(512)))
1919
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512dq")))
2020

2121
static __inline __mmask8 __DEFAULT_FN_ATTRS

‎clang/lib/Headers/avx512fintrin.h

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -167,7 +167,7 @@ typedef enum
167167
} _MM_MANTISSA_SIGN_ENUM;
168168

169169
/* Define the default attributes for the functions in this file. */
170-
#define __DEFAULT_FN_ATTRS512 __attribute__((__always_inline__, __nodebug__, __target__("avx512f,evex512"), __min_vector_width__(512)))
170+
#define __DEFAULT_FN_ATTRS512 __attribute__((__always_inline__, __nodebug__, __target__("avx512f"), __min_vector_width__(512)))
171171
#define __DEFAULT_FN_ATTRS128 __attribute__((__always_inline__, __nodebug__, __target__("avx512f"), __min_vector_width__(128)))
172172
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512f")))
173173

‎clang/lib/Headers/avx512fp16intrin.h

Lines changed: 2 additions & 2 deletions
Original file line numberDiff line numberDiff line change
@@ -22,8 +22,8 @@ typedef _Float16 __m512h_u __attribute__((__vector_size__(64), __aligned__(1)));
2222

2323
/* Define the default attributes for the functions in this file. */
2424
#define __DEFAULT_FN_ATTRS512 \
25-
__attribute__((__always_inline__, __nodebug__, \
26-
__target__("avx512fp16,evex512"), __min_vector_width__(512)))
25+
__attribute__((__always_inline__, __nodebug__, __target__("avx512fp16"), \
26+
__min_vector_width__(512)))
2727
#define __DEFAULT_FN_ATTRS256 \
2828
__attribute__((__always_inline__, __nodebug__, __target__("avx512fp16"), \
2929
__min_vector_width__(256)))

‎clang/lib/Headers/avx512ifmaintrin.h

Lines changed: 1 addition & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -15,9 +15,7 @@
1515
#define __IFMAINTRIN_H
1616

1717
/* Define the default attributes for the functions in this file. */
18-
#define __DEFAULT_FN_ATTRS \
19-
__attribute__((__always_inline__, __nodebug__, \
20-
__target__("avx512ifma,evex512"), __min_vector_width__(512)))
18+
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512ifma"), __min_vector_width__(512)))
2119

2220
static __inline__ __m512i __DEFAULT_FN_ATTRS
2321
_mm512_madd52hi_epu64 (__m512i __X, __m512i __Y, __m512i __Z)

‎clang/lib/Headers/avx512vbmi2intrin.h

Lines changed: 1 addition & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -15,7 +15,7 @@
1515
#define __AVX512VBMI2INTRIN_H
1616

1717
/* Define the default attributes for the functions in this file. */
18-
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512vbmi2,evex512"), __min_vector_width__(512)))
18+
#define __DEFAULT_FN_ATTRS __attribute__((__always_inline__, __nodebug__, __target__("avx512vbmi2"), __min_vector_width__(512)))
1919

2020

2121
static __inline__ __m512i __DEFAULT_FN_ATTRS

0 commit comments

Comments
 (0)