maxjhandsome
/
llvm-project
forked from OSchip/llvm-project
1
0
Fork 0
Code Issues Pull Requests Packages Releases Wiki Activity

[RISCV] Use clang_builtin_alias for all RISCV vector intrinsics. 

Previously we used builtin_alias for overloaded intrinsics, but
macros for the non-overloaded version. This patch changes the
non-overloaded versions to also use builtin_alias, but without
the overloadable attribute.

Reviewed By: khchen, HsiangKai

Differential Revision: https://reviews.llvm.org/D112020
This commit is contained in:
Craig Topper 2021-10-20 07:54:05 -07:00
parent 16be17ad4b
commit a29dfc089d
1 changed files with 23 additions and 19 deletions
Show Stats Download Patch File Download Diff File Expand all files Collapse all files

42
clang/utils/TableGen/RISCVVEmitter.cpp
View File

@ -198,7 +198,7 @@ public:
void emitCodeGenSwitchBody(raw_ostream &o) const; void emitCodeGenSwitchBody(raw_ostream &o) const;
// Emit the macros for mapping C/C++ intrinsic function to builtin functions. // Emit the macros for mapping C/C++ intrinsic function to builtin functions.
void emitIntrinsicMacro(raw_ostream &o) const; void emitIntrinsicFuncDef(raw_ostream &o) const;
// Emit the mangled function definition. // Emit the mangled function definition.
void emitMangledFuncDef(raw_ostream &o) const; void emitMangledFuncDef(raw_ostream &o) const;
@ -855,34 +855,30 @@ void RVVIntrinsic::emitCodeGenSwitchBody(raw_ostream &OS) const {
OS << " break;\n"; OS << " break;\n";
} }
void RVVIntrinsic::emitIntrinsicMacro(raw_ostream &OS) const { void RVVIntrinsic::emitIntrinsicFuncDef(raw_ostream &OS) const {
OS << "#define " << getName() << "("; OS << "__attribute__((__clang_builtin_alias__(";
OS << "__builtin_rvv_" << getName() << ")))\n";
OS << OutputType->getTypeStr() << " " << getName() << "(";
// Emit function arguments
if (!InputTypes.empty()) { if (!InputTypes.empty()) {
ListSeparator LS; ListSeparator LS;
for (unsigned i = 0, e = InputTypes.size(); i != e; ++i) for (unsigned i = 0; i < InputTypes.size(); ++i)
OS << LS << "op" << i; OS << LS << InputTypes[i]->getTypeStr();
} }
OS << ") \\\n"; OS << ");\n";
OS << "__builtin_rvv_" << getName() << "(";
if (!InputTypes.empty()) {
ListSeparator LS;
for (unsigned i = 0, e = InputTypes.size(); i != e; ++i)
OS << LS << "(" << InputTypes[i]->getTypeStr() << ")(op" << i << ")";
}
OS << ")\n";
} }
void RVVIntrinsic::emitMangledFuncDef(raw_ostream &OS) const { void RVVIntrinsic::emitMangledFuncDef(raw_ostream &OS) const {
OS << "__attribute__((clang_builtin_alias("; OS << "__attribute__((__clang_builtin_alias__(";
OS << "__builtin_rvv_" << getName() << ")))\n"; OS << "__builtin_rvv_" << getName() << ")))\n";
OS << OutputType->getTypeStr() << " " << getMangledName() << "("; OS << OutputType->getTypeStr() << " " << getMangledName() << "(";
// Emit function arguments // Emit function arguments
if (!InputTypes.empty()) { if (!InputTypes.empty()) {
ListSeparator LS; ListSeparator LS;
for (unsigned i = 0; i < InputTypes.size(); ++i) for (unsigned i = 0; i < InputTypes.size(); ++i)
OS << LS << InputTypes[i]->getTypeStr() << " op" << i; OS << LS << InputTypes[i]->getTypeStr();
} }
OS << ");\n\n"; OS << ");\n";
} }
//===----------------------------------------------------------------------===// //===----------------------------------------------------------------------===//
@ -980,24 +976,32 @@ void RVVEmitter::createHeader(raw_ostream &OS) {
return A->getRISCVExtensions() < B->getRISCVExtensions(); return A->getRISCVExtensions() < B->getRISCVExtensions();
}); });
OS << "#define __rvv_ai static __inline__ "
"__attribute__((__always_inline__, __nodebug__))\n";
// Print intrinsic functions with macro // Print intrinsic functions with macro
emitArchMacroAndBody(Defs, OS, [](raw_ostream &OS, const RVVIntrinsic &Inst) { emitArchMacroAndBody(Defs, OS, [](raw_ostream &OS, const RVVIntrinsic &Inst) {
Inst.emitIntrinsicMacro(OS); OS << "__rvv_ai ";
Inst.emitIntrinsicFuncDef(OS);
}); });
OS << "#undef __rvv_ai\n\n";
OS << "#define __riscv_v_intrinsic_overloading 1\n"; OS << "#define __riscv_v_intrinsic_overloading 1\n";
// Print Overloaded APIs // Print Overloaded APIs
OS << "#define __rvv_overloaded static inline " OS << "#define __rvv_aio static __inline__ "
"__attribute__((__always_inline__, __nodebug__, __overloadable__))\n"; "__attribute__((__always_inline__, __nodebug__, __overloadable__))\n";
emitArchMacroAndBody(Defs, OS, [](raw_ostream &OS, const RVVIntrinsic &Inst) { emitArchMacroAndBody(Defs, OS, [](raw_ostream &OS, const RVVIntrinsic &Inst) {
if (!Inst.isMask() && !Inst.hasNoMaskedOverloaded()) if (!Inst.isMask() && !Inst.hasNoMaskedOverloaded())
return; return;
OS << "__rvv_overloaded "; OS << "__rvv_aio ";
Inst.emitMangledFuncDef(OS); Inst.emitMangledFuncDef(OS);
}); });
OS << "#undef __rvv_aio\n";
OS << "\n#ifdef __cplusplus\n"; OS << "\n#ifdef __cplusplus\n";
OS << "}\n"; OS << "}\n";
OS << "#endif // __cplusplus\n"; OS << "#endif // __cplusplus\n";