Skip to content

Commit c29966b

Browse files
danliew-appledanliew-apple
committed
([Automerger: llvm.org/main -> next] conflict merging 9189660 ([RISCV] RISCV vector calling convention (1/2) (llvm#77560)))
Merge commit '91896607ffb8' from llvm.org/main into next Conflicts: llvm/include/llvm/BinaryFormat/Dwarf.def rdar://125488167
2 parents 7a0d3a7 + 9189660 commit c29966b

29 files changed

+409
-50
lines changed

‎clang/include/clang-c/Index.h

Lines changed: 1 addition & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -2991,6 +2991,7 @@ enum CXCallingConv {
29912991
CXCallingConv_AArch64SVEPCS = 18,
29922992
CXCallingConv_M68kRTD = 19,
29932993
CXCallingConv_PreserveNone = 20,
2994+
CXCallingConv_RISCVVectorCall = 21,
29942995

29952996
CXCallingConv_Invalid = 100,
29962997
CXCallingConv_Unexposed = 200

‎clang/include/clang/Basic/Attr.td

Lines changed: 7 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -3027,6 +3027,13 @@ def PreserveNone : DeclOrTypeAttr, TargetSpecificAttr<TargetAnyX86> {
30273027
let Documentation = [PreserveNoneDocs];
30283028
}
30293029

3030+
def RISCVVectorCC: DeclOrTypeAttr, TargetSpecificAttr<TargetRISCV> {
3031+
let Spellings = [CXX11<"riscv", "vector_cc">,
3032+
C23<"riscv", "vector_cc">,
3033+
Clang<"riscv_vector_cc">];
3034+
let Documentation = [RISCVVectorCCDocs];
3035+
}
3036+
30303037
def Target : InheritableAttr {
30313038
let Spellings = [GCC<"target">];
30323039
let Args = [StringArgument<"featuresStr">];

‎clang/include/clang/Basic/AttrDocs.td

Lines changed: 11 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -5653,6 +5653,17 @@ for clang builtin functions.
56535653
}];
56545654
}
56555655

5656+
def RISCVVectorCCDocs : Documentation {
5657+
let Category = DocCatCallingConvs;
5658+
let Heading = "riscv::vector_cc, riscv_vector_cc, clang::riscv_vector_cc";
5659+
let Content = [{
5660+
The ``riscv_vector_cc`` attribute can be applied to a function. It preserves 15
5661+
registers namely, v1-v7 and v24-v31 as callee-saved. Callers thus don't need
5662+
to save these registers before function calls, and callees only need to save
5663+
them if they use them.
5664+
}];
5665+
}
5666+
56565667
def PreferredNameDocs : Documentation {
56575668
let Category = DocCatDecl;
56585669
let Content = [{

‎clang/include/clang/Basic/Specifiers.h

Lines changed: 22 additions & 21 deletions
Original file line numberDiff line numberDiff line change
@@ -273,29 +273,30 @@ namespace clang {
273273

274274
/// CallingConv - Specifies the calling convention that a function uses.
275275
enum CallingConv {
276-
CC_C, // __attribute__((cdecl))
277-
CC_X86StdCall, // __attribute__((stdcall))
278-
CC_X86FastCall, // __attribute__((fastcall))
279-
CC_X86ThisCall, // __attribute__((thiscall))
280-
CC_X86VectorCall, // __attribute__((vectorcall))
281-
CC_X86Pascal, // __attribute__((pascal))
282-
CC_Win64, // __attribute__((ms_abi))
283-
CC_X86_64SysV, // __attribute__((sysv_abi))
284-
CC_X86RegCall, // __attribute__((regcall))
285-
CC_AAPCS, // __attribute__((pcs("aapcs")))
286-
CC_AAPCS_VFP, // __attribute__((pcs("aapcs-vfp")))
287-
CC_IntelOclBicc, // __attribute__((intel_ocl_bicc))
288-
CC_SpirFunction, // default for OpenCL functions on SPIR target
289-
CC_OpenCLKernel, // inferred for OpenCL kernels
290-
CC_Swift, // __attribute__((swiftcall))
276+
CC_C, // __attribute__((cdecl))
277+
CC_X86StdCall, // __attribute__((stdcall))
278+
CC_X86FastCall, // __attribute__((fastcall))
279+
CC_X86ThisCall, // __attribute__((thiscall))
280+
CC_X86VectorCall, // __attribute__((vectorcall))
281+
CC_X86Pascal, // __attribute__((pascal))
282+
CC_Win64, // __attribute__((ms_abi))
283+
CC_X86_64SysV, // __attribute__((sysv_abi))
284+
CC_X86RegCall, // __attribute__((regcall))
285+
CC_AAPCS, // __attribute__((pcs("aapcs")))
286+
CC_AAPCS_VFP, // __attribute__((pcs("aapcs-vfp")))
287+
CC_IntelOclBicc, // __attribute__((intel_ocl_bicc))
288+
CC_SpirFunction, // default for OpenCL functions on SPIR target
289+
CC_OpenCLKernel, // inferred for OpenCL kernels
290+
CC_Swift, // __attribute__((swiftcall))
291291
CC_SwiftAsync, // __attribute__((swiftasynccall))
292-
CC_PreserveMost, // __attribute__((preserve_most))
293-
CC_PreserveAll, // __attribute__((preserve_all))
292+
CC_PreserveMost, // __attribute__((preserve_most))
293+
CC_PreserveAll, // __attribute__((preserve_all))
294294
CC_AArch64VectorCall, // __attribute__((aarch64_vector_pcs))
295-
CC_AArch64SVEPCS, // __attribute__((aarch64_sve_pcs))
296-
CC_AMDGPUKernelCall, // __attribute__((amdgpu_kernel))
297-
CC_M68kRTD, // __attribute__((m68k_rtd))
298-
CC_PreserveNone, // __attribute__((preserve_none))
295+
CC_AArch64SVEPCS, // __attribute__((aarch64_sve_pcs))
296+
CC_AMDGPUKernelCall, // __attribute__((amdgpu_kernel))
297+
CC_M68kRTD, // __attribute__((m68k_rtd))
298+
CC_PreserveNone, // __attribute__((preserve_none))
299+
CC_RISCVVectorCall, // __attribute__((riscv_vector_cc))
299300
};
300301

301302
/// Checks whether the given calling convention supports variadic

‎clang/lib/AST/ItaniumMangle.cpp

Lines changed: 1 addition & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -3448,6 +3448,7 @@ StringRef CXXNameMangler::getCallingConvQualifierName(CallingConv CC) {
34483448
case CC_PreserveAll:
34493449
case CC_M68kRTD:
34503450
case CC_PreserveNone:
3451+
case CC_RISCVVectorCall:
34513452
// FIXME: we should be mangling all of the above.
34523453
return "";
34533454

‎clang/lib/AST/Type.cpp

Lines changed: 4 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -3481,6 +3481,9 @@ StringRef FunctionType::getNameForCallConv(CallingConv CC) {
34813481
case CC_PreserveAll: return "preserve_all";
34823482
case CC_M68kRTD: return "m68k_rtd";
34833483
case CC_PreserveNone: return "preserve_none";
3484+
// clang-format off
3485+
case CC_RISCVVectorCall: return "riscv_vector_cc";
3486+
// clang-format on
34843487
}
34853488

34863489
llvm_unreachable("Invalid calling convention.");
@@ -4071,6 +4074,7 @@ bool AttributedType::isCallingConv() const {
40714074
case attr::PreserveAll:
40724075
case attr::M68kRTD:
40734076
case attr::PreserveNone:
4077+
case attr::RISCVVectorCC:
40744078
return true;
40754079
}
40764080
llvm_unreachable("invalid attr kind");

‎clang/lib/AST/TypePrinter.cpp

Lines changed: 6 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -1075,6 +1075,9 @@ void TypePrinter::printFunctionAfter(const FunctionType::ExtInfo &Info,
10751075
case CC_PreserveNone:
10761076
OS << " __attribute__((preserve_none))";
10771077
break;
1078+
case CC_RISCVVectorCall:
1079+
OS << "__attribute__((riscv_vector_cc))";
1080+
break;
10781081
}
10791082
}
10801083

@@ -1972,6 +1975,9 @@ void TypePrinter::printAttributedAfter(const AttributedType *T,
19721975
case attr::PreserveNone:
19731976
OS << "preserve_none";
19741977
break;
1978+
case attr::RISCVVectorCC:
1979+
OS << "riscv_vector_cc";
1980+
break;
19751981
case attr::NoDeref:
19761982
OS << "noderef";
19771983
break;

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

Lines changed: 11 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -467,3 +467,14 @@ ParsedTargetAttr RISCVTargetInfo::parseTargetAttr(StringRef Features) const {
467467
}
468468
return Ret;
469469
}
470+
471+
TargetInfo::CallingConvCheckResult
472+
RISCVTargetInfo::checkCallingConvention(CallingConv CC) const {
473+
switch (CC) {
474+
default:
475+
return CCCR_Warning;
476+
case CC_C:
477+
case CC_RISCVVectorCall:
478+
return CCCR_OK;
479+
}
480+
}

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

Lines changed: 2 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -110,6 +110,8 @@ class RISCVTargetInfo : public TargetInfo {
110110

111111
bool hasBFloat16Type() const override { return true; }
112112

113+
CallingConvCheckResult checkCallingConvention(CallingConv CC) const override;
114+
113115
bool useFP16ConversionIntrinsics() const override {
114116
return false;
115117
}

‎clang/lib/CodeGen/CGCall.cpp

Lines changed: 6 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -74,6 +74,9 @@ unsigned CodeGenTypes::ClangCallConvToLLVMCallConv(CallingConv CC) {
7474
case CC_SwiftAsync: return llvm::CallingConv::SwiftTail;
7575
case CC_M68kRTD: return llvm::CallingConv::M68k_RTD;
7676
case CC_PreserveNone: return llvm::CallingConv::PreserveNone;
77+
// clang-format off
78+
case CC_RISCVVectorCall: return llvm::CallingConv::RISCV_VectorCall;
79+
// clang-format on
7780
}
7881
}
7982

@@ -260,6 +263,9 @@ static CallingConv getCallingConventionForDecl(const ObjCMethodDecl *D,
260263
if (D->hasAttr<PreserveNoneAttr>())
261264
return CC_PreserveNone;
262265

266+
if (D->hasAttr<RISCVVectorCCAttr>())
267+
return CC_RISCVVectorCall;
268+
263269
return CC_C;
264270
}
265271

‎clang/lib/CodeGen/CGDebugInfo.cpp

Lines changed: 2 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -1468,6 +1468,8 @@ static unsigned getDwarfCC(CallingConv CC) {
14681468
return llvm::dwarf::DW_CC_LLVM_M68kRTD;
14691469
case CC_PreserveNone:
14701470
return llvm::dwarf::DW_CC_LLVM_PreserveNone;
1471+
case CC_RISCVVectorCall:
1472+
return llvm::dwarf::DW_CC_LLVM_RISCVVectorCall;
14711473
}
14721474
return 0;
14731475
}

‎clang/lib/Sema/SemaDeclAttr.cpp

Lines changed: 7 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -5280,6 +5280,9 @@ static void handleCallConvAttr(Sema &S, Decl *D, const ParsedAttr &AL) {
52805280
case ParsedAttr::AT_PreserveNone:
52815281
D->addAttr(::new (S.Context) PreserveNoneAttr(S.Context, AL));
52825282
return;
5283+
case ParsedAttr::AT_RISCVVectorCC:
5284+
D->addAttr(::new (S.Context) RISCVVectorCCAttr(S.Context, AL));
5285+
return;
52835286
default:
52845287
llvm_unreachable("unexpected attribute kind");
52855288
}
@@ -5484,6 +5487,9 @@ bool Sema::CheckCallingConvAttr(const ParsedAttr &Attrs, CallingConv &CC,
54845487
case ParsedAttr::AT_PreserveNone:
54855488
CC = CC_PreserveNone;
54865489
break;
5490+
case ParsedAttr::AT_RISCVVectorCC:
5491+
CC = CC_RISCVVectorCall;
5492+
break;
54875493
default: llvm_unreachable("unexpected attribute kind");
54885494
}
54895495

@@ -9658,6 +9664,7 @@ ProcessDeclAttribute(Sema &S, Scope *scope, Decl *D, const ParsedAttr &AL,
96589664
case ParsedAttr::AT_AMDGPUKernelCall:
96599665
case ParsedAttr::AT_M68kRTD:
96609666
case ParsedAttr::AT_PreserveNone:
9667+
case ParsedAttr::AT_RISCVVectorCC:
96619668
handleCallConvAttr(S, D, AL);
96629669
break;
96639670
case ParsedAttr::AT_Suppress:

‎clang/lib/Sema/SemaType.cpp

Lines changed: 4 additions & 1 deletion
Original file line numberDiff line numberDiff line change
@@ -138,7 +138,8 @@ static void diagnoseBadTypeAttribute(Sema &S, const ParsedAttr &attr,
138138
case ParsedAttr::AT_PreserveMost: \
139139
case ParsedAttr::AT_PreserveAll: \
140140
case ParsedAttr::AT_M68kRTD: \
141-
case ParsedAttr::AT_PreserveNone
141+
case ParsedAttr::AT_PreserveNone: \
142+
case ParsedAttr::AT_RISCVVectorCC
142143

143144
// Function type attributes.
144145
#define FUNCTION_TYPE_ATTRS_CASELIST \
@@ -7940,6 +7941,8 @@ static Attr *getCCTypeAttr(ASTContext &Ctx, ParsedAttr &Attr) {
79407941
return createSimpleAttr<M68kRTDAttr>(Ctx, Attr);
79417942
case ParsedAttr::AT_PreserveNone:
79427943
return createSimpleAttr<PreserveNoneAttr>(Ctx, Attr);
7944+
case ParsedAttr::AT_RISCVVectorCC:
7945+
return createSimpleAttr<RISCVVectorCCAttr>(Ctx, Attr);
79437946
}
79447947
llvm_unreachable("unexpected attribute kind!");
79457948
}

‎clang/test/CodeGen/RISCV/riscv-vector-callingconv-llvm-ir.c

Lines changed: 34 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,34 @@
1+
// REQUIRES: riscv-registered-target
2+
// RUN: %clang_cc1 -triple riscv64 -target-feature +v \
3+
// RUN: -emit-llvm %s -o - | FileCheck -check-prefix=CHECK-LLVM %s
4+
// RUN: %clang_cc1 -std=c23 -triple riscv64 -target-feature +v \
5+
// RUN: -emit-llvm %s -o - | FileCheck -check-prefix=CHECK-LLVM %s
6+
7+
#include <riscv_vector.h>
8+
9+
// CHECK-LLVM: call riscv_vector_cc <vscale x 2 x i32> @bar
10+
vint32m1_t __attribute__((riscv_vector_cc)) bar(vint32m1_t input);
11+
vint32m1_t test_vector_cc_attr(vint32m1_t input, int32_t *base, size_t vl) {
12+
vint32m1_t val = __riscv_vle32_v_i32m1(base, vl);
13+
vint32m1_t ret = bar(input);
14+
__riscv_vse32_v_i32m1(base, val, vl);
15+
return ret;
16+
}
17+
18+
// CHECK-LLVM: call riscv_vector_cc <vscale x 2 x i32> @bar
19+
[[riscv::vector_cc]] vint32m1_t bar(vint32m1_t input);
20+
vint32m1_t test_vector_cc_attr2(vint32m1_t input, int32_t *base, size_t vl) {
21+
vint32m1_t val = __riscv_vle32_v_i32m1(base, vl);
22+
vint32m1_t ret = bar(input);
23+
__riscv_vse32_v_i32m1(base, val, vl);
24+
return ret;
25+
}
26+
27+
// CHECK-LLVM: call <vscale x 2 x i32> @baz
28+
vint32m1_t baz(vint32m1_t input);
29+
vint32m1_t test_no_vector_cc_attr(vint32m1_t input, int32_t *base, size_t vl) {
30+
vint32m1_t val = __riscv_vle32_v_i32m1(base, vl);
31+
vint32m1_t ret = baz(input);
32+
__riscv_vse32_v_i32m1(base, val, vl);
33+
return ret;
34+
}

‎clang/test/CodeGen/RISCV/riscv-vector-callingconv-llvm-ir.cpp

Lines changed: 32 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,32 @@
1+
// REQUIRES: riscv-registered-target
2+
// RUN: %clang_cc1 -std=c++11 -triple riscv64 -target-feature +v \
3+
// RUN: -emit-llvm %s -o - | FileCheck -check-prefix=CHECK-LLVM %s
4+
5+
#include <riscv_vector.h>
6+
7+
// CHECK-LLVM: call riscv_vector_cc <vscale x 2 x i32> @_Z3baru15__rvv_int32m1_t
8+
vint32m1_t __attribute__((riscv_vector_cc)) bar(vint32m1_t input);
9+
vint32m1_t test_vector_cc_attr(vint32m1_t input, int32_t *base, size_t vl) {
10+
vint32m1_t val = __riscv_vle32_v_i32m1(base, vl);
11+
vint32m1_t ret = bar(input);
12+
__riscv_vse32_v_i32m1(base, val, vl);
13+
return ret;
14+
}
15+
16+
// CHECK-LLVM: call riscv_vector_cc <vscale x 2 x i32> @_Z3baru15__rvv_int32m1_t
17+
[[riscv::vector_cc]] vint32m1_t bar(vint32m1_t input);
18+
vint32m1_t test_vector_cc_attr2(vint32m1_t input, int32_t *base, size_t vl) {
19+
vint32m1_t val = __riscv_vle32_v_i32m1(base, vl);
20+
vint32m1_t ret = bar(input);
21+
__riscv_vse32_v_i32m1(base, val, vl);
22+
return ret;
23+
}
24+
25+
// CHECK-LLVM: call <vscale x 2 x i32> @_Z3bazu15__rvv_int32m1_t
26+
vint32m1_t baz(vint32m1_t input);
27+
vint32m1_t test_no_vector_cc_attr(vint32m1_t input, int32_t *base, size_t vl) {
28+
vint32m1_t val = __riscv_vle32_v_i32m1(base, vl);
29+
vint32m1_t ret = baz(input);
30+
__riscv_vse32_v_i32m1(base, val, vl);
31+
return ret;
32+
}

‎clang/test/CodeGen/RISCV/riscv-vector-callingconv.c

Lines changed: 17 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,17 @@
1+
// RUN: %clang_cc1 %s -std=c23 -triple riscv64 -target-feature +v -verify
2+
3+
__attribute__((riscv_vector_cc)) int var; // expected-warning {{'riscv_vector_cc' only applies to function types; type here is 'int'}}
4+
5+
__attribute__((riscv_vector_cc)) void func();
6+
__attribute__((riscv_vector_cc(1))) void func_invalid(); // expected-error {{'riscv_vector_cc' attribute takes no arguments}}
7+
8+
void test_no_attribute(int); // expected-note {{previous declaration is here}}
9+
void __attribute__((riscv_vector_cc)) test_no_attribute(int x) { } // expected-error {{function declared 'riscv_vector_cc' here was previously declared without calling convention}}
10+
11+
[[riscv::vector_cc]] int var2; // expected-warning {{'vector_cc' only applies to function types; type here is 'int'}}
12+
13+
[[riscv::vector_cc]] void func2();
14+
[[riscv::vector_cc(1)]] void func_invalid2(); // expected-error {{'vector_cc' attribute takes no arguments}}
15+
16+
void test_no_attribute2(int); // expected-note {{previous declaration is here}}
17+
[[riscv::vector_cc]] void test_no_attribute2(int x) { } // expected-error {{function declared 'riscv_vector_cc' here was previously declared without calling convention}}

‎clang/test/CodeGen/RISCV/riscv-vector-callingconv.cpp

Lines changed: 35 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -0,0 +1,35 @@
1+
// RUN: %clang_cc1 %s -triple riscv64 -target-feature +v -verify
2+
3+
__attribute__((riscv_vector_cc)) int var; // expected-warning {{'riscv_vector_cc' only applies to function types; type here is 'int'}}
4+
5+
__attribute__((riscv_vector_cc)) void func();
6+
__attribute__((riscv_vector_cc(1))) void func_invalid(); // expected-error {{'riscv_vector_cc' attribute takes no arguments}}
7+
8+
void test_no_attribute(int); // expected-note {{previous declaration is here}}
9+
void __attribute__((riscv_vector_cc)) test_no_attribute(int x) { } // expected-error {{function declared 'riscv_vector_cc' here was previously declared without calling convention}}
10+
11+
class test_cc {
12+
__attribute__((riscv_vector_cc)) void member_func();
13+
};
14+
15+
void test_lambda() {
16+
__attribute__((riscv_vector_cc)) auto lambda = []() { // expected-warning {{'riscv_vector_cc' only applies to function types; type here is 'auto'}}
17+
};
18+
}
19+
20+
[[riscv::vector_cc]] int var2; // expected-warning {{'vector_cc' only applies to function types; type here is 'int'}}
21+
22+
[[riscv::vector_cc]] void func2();
23+
[[riscv::vector_cc(1)]] void func_invalid2(); // expected-error {{'vector_cc' attribute takes no arguments}}
24+
25+
void test_no_attribute2(int); // expected-note {{previous declaration is here}}
26+
[[riscv::vector_cc]] void test_no_attribute2(int x) { } // expected-error {{function declared 'riscv_vector_cc' here was previously declared without calling convention}}
27+
28+
class test_cc2 {
29+
[[riscv::vector_cc]] void member_func();
30+
};
31+
32+
void test_lambda2() {
33+
[[riscv::vector_cc]] auto lambda = []() { // expected-warning {{'vector_cc' only applies to function types; type here is 'auto'}}
34+
};
35+
}

‎clang/tools/libclang/CXType.cpp

Lines changed: 1 addition & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -680,6 +680,7 @@ CXCallingConv clang_getFunctionTypeCallingConv(CXType X) {
680680
TCALLINGCONV(PreserveAll);
681681
TCALLINGCONV(M68kRTD);
682682
TCALLINGCONV(PreserveNone);
683+
TCALLINGCONV(RISCVVectorCall);
683684
case CC_SpirFunction: return CXCallingConv_Unexposed;
684685
case CC_AMDGPUKernelCall: return CXCallingConv_Unexposed;
685686
case CC_OpenCLKernel: return CXCallingConv_Unexposed;

‎llvm/include/llvm/AsmParser/LLToken.h

Lines changed: 1 addition & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -181,6 +181,7 @@ enum Kind {
181181
kw_tailcc,
182182
kw_m68k_rtdcc,
183183
kw_graalcc,
184+
kw_riscv_vector_cc,
184185

185186
// Attributes:
186187
kw_attributes,

‎llvm/include/llvm/BinaryFormat/Dwarf.def

Lines changed: 1 addition & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -1046,6 +1046,7 @@ HANDLE_DW_CC(0xcb, LLVM_X86RegCall)
10461046
HANDLE_DW_CC(0xcc, LLVM_M68kRTD)
10471047
HANDLE_DW_CC(0xcd, LLVM_SwiftTail)
10481048
HANDLE_DW_CC(0xce, LLVM_PreserveNone)
1049+
HANDLE_DW_CC(0xcf, LLVM_RISCVVectorCall)
10491050
// From GCC source code (include/dwarf2.h): This DW_CC_ value is not currently
10501051
// generated by any toolchain. It is used internally to GDB to indicate OpenCL
10511052
// C functions that have been compiled with the IBM XL C for OpenCL compiler and

‎llvm/include/llvm/IR/CallingConv.h

Lines changed: 3 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -264,6 +264,9 @@ namespace CallingConv {
264264
/// except that the first parameter is mapped to x9.
265265
ARM64EC_Thunk_Native = 109,
266266

267+
/// Calling convention used for RISC-V V-extension.
268+
RISCV_VectorCall = 110,
269+
267270
/// The highest possible ID. Must be some 2^k - 1.
268271
MaxID = 1023
269272
};

0 commit comments

Comments
 (0)