Home
last modified time | relevance | path

Searched refs:BuiltinID (Results 1 – 25 of 68) sorted by relevance

123

/freebsd/contrib/llvm-project/clang/lib/Sema/
H A DSemaARM.cpp26 bool SemaARM::BuiltinARMMemoryTaggingCall(unsigned BuiltinID, in BuiltinARMMemoryTaggingCall() argument
30 if (BuiltinID == AArch64::BI__builtin_arm_irg) { in BuiltinARMMemoryTaggingCall()
58 if (BuiltinID == AArch64::BI__builtin_arm_addg) { in BuiltinARMMemoryTaggingCall()
79 if (BuiltinID == AArch64::BI__builtin_arm_gmi) { in BuiltinARMMemoryTaggingCall()
101 if (BuiltinID == AArch64::BI__builtin_arm_ldg || in BuiltinARMMemoryTaggingCall()
102 BuiltinID == AArch64::BI__builtin_arm_stg) { in BuiltinARMMemoryTaggingCall()
117 if (BuiltinID == AArch64::BI__builtin_arm_ldg) in BuiltinARMMemoryTaggingCall()
122 if (BuiltinID == AArch64::BI__builtin_arm_subp) { in BuiltinARMMemoryTaggingCall()
188 bool SemaARM::BuiltinARMSpecialReg(unsigned BuiltinID, CallExpr *TheCall, in BuiltinARMSpecialReg() argument
191 bool IsARMBuiltin = BuiltinID == ARM::BI__builtin_arm_rsr64 || in BuiltinARMSpecialReg()
[all …]
H A DSemaBPF.cpp111 bool SemaBPF::CheckBPFBuiltinFunctionCall(unsigned BuiltinID, in CheckBPFBuiltinFunctionCall() argument
113 assert((BuiltinID == BPF::BI__builtin_preserve_field_info || in CheckBPFBuiltinFunctionCall()
114 BuiltinID == BPF::BI__builtin_btf_type_id || in CheckBPFBuiltinFunctionCall()
115 BuiltinID == BPF::BI__builtin_preserve_type_info || in CheckBPFBuiltinFunctionCall()
116 BuiltinID == BPF::BI__builtin_preserve_enum_value) && in CheckBPFBuiltinFunctionCall()
127 if (BuiltinID == BPF::BI__builtin_preserve_field_info) in CheckBPFBuiltinFunctionCall()
129 else if (BuiltinID == BPF::BI__builtin_btf_type_id) in CheckBPFBuiltinFunctionCall()
131 else if (BuiltinID == BPF::BI__builtin_preserve_type_info) in CheckBPFBuiltinFunctionCall()
143 if (BuiltinID == BPF::BI__builtin_preserve_field_info) { in CheckBPFBuiltinFunctionCall()
148 } else if (BuiltinID == BPF::BI__builtin_preserve_type_info) { in CheckBPFBuiltinFunctionCall()
[all …]
H A DSemaHexagon.cpp24 bool SemaHexagon::CheckHexagonBuiltinArgument(unsigned BuiltinID, in CheckHexagonBuiltinArgument() argument
33 unsigned BuiltinID; in CheckHexagonBuiltinArgument() member
253 return LHS.BuiltinID < RHS.BuiltinID; in CheckHexagonBuiltinArgument()
259 Infos, [=](const BuiltinInfo &BI) { return BI.BuiltinID < BuiltinID; }); in CheckHexagonBuiltinArgument()
260 if (F == std::end(Infos) || F->BuiltinID != BuiltinID) in CheckHexagonBuiltinArgument()
285 bool SemaHexagon::CheckHexagonBuiltinFunctionCall(unsigned BuiltinID, in CheckHexagonBuiltinFunctionCall() argument
287 return CheckHexagonBuiltinArgument(BuiltinID, TheCall); in CheckHexagonBuiltinFunctionCall()
H A DSemaMIPS.cpp26 unsigned BuiltinID, in CheckMipsBuiltinFunctionCall() argument
28 return CheckMipsBuiltinCpu(TI, BuiltinID, TheCall) || in CheckMipsBuiltinFunctionCall()
29 CheckMipsBuiltinArgument(BuiltinID, TheCall); in CheckMipsBuiltinFunctionCall()
32 bool SemaMIPS::CheckMipsBuiltinCpu(const TargetInfo &TI, unsigned BuiltinID, in CheckMipsBuiltinCpu() argument
35 if (Mips::BI__builtin_mips_addu_qb <= BuiltinID && in CheckMipsBuiltinCpu()
36 BuiltinID <= Mips::BI__builtin_mips_lwx) { in CheckMipsBuiltinCpu()
41 if (Mips::BI__builtin_mips_absq_s_qb <= BuiltinID && in CheckMipsBuiltinCpu()
42 BuiltinID <= Mips::BI__builtin_mips_subuh_r_qb) { in CheckMipsBuiltinCpu()
48 if (Mips::BI__builtin_msa_add_a_b <= BuiltinID && in CheckMipsBuiltinCpu()
49 BuiltinID <= Mips::BI__builtin_msa_xori_b) { in CheckMipsBuiltinCpu()
[all …]
H A DSemaPPC.cpp57 static bool isPPC_64Builtin(unsigned BuiltinID) { in isPPC_64Builtin() argument
59 switch (BuiltinID) { in isPPC_64Builtin()
97 unsigned BuiltinID, in CheckPPCBuiltinFunctionCall() argument
102 if (isPPC_64Builtin(BuiltinID) && !IsTarget64Bit) in CheckPPCBuiltinFunctionCall()
106 switch (BuiltinID) { in CheckPPCBuiltinFunctionCall()
232 (BuiltinID == PPC::BI__builtin_ppc_maxfe || in CheckPPCBuiltinFunctionCall()
233 BuiltinID == PPC::BI__builtin_ppc_minfe)) in CheckPPCBuiltinFunctionCall()
239 if (BuiltinID == PPC::BI__builtin_ppc_maxfl || in CheckPPCBuiltinFunctionCall()
240 BuiltinID == PPC::BI__builtin_ppc_minfl) in CheckPPCBuiltinFunctionCall()
242 else if (BuiltinID == PPC::BI__builtin_ppc_maxfs || in CheckPPCBuiltinFunctionCall()
[all …]
H A DSemaSPIRV.cpp141 unsigned BuiltinID, in CheckSPIRVBuiltinFunctionCall() argument
143 if (BuiltinID >= SPIRV::FirstVKBuiltin && BuiltinID <= SPIRV::LastVKBuiltin && in CheckSPIRVBuiltinFunctionCall()
148 if (BuiltinID >= SPIRV::FirstCLBuiltin && BuiltinID <= SPIRV::LastTSBuiltin && in CheckSPIRVBuiltinFunctionCall()
155 switch (BuiltinID) { in CheckSPIRVBuiltinFunctionCall()
H A DSemaNVPTX.cpp22 unsigned BuiltinID, in CheckNVPTXBuiltinFunctionCall() argument
24 switch (BuiltinID) { in CheckNVPTXBuiltinFunctionCall()
H A DSemaSystemZ.cpp24 bool SemaSystemZ::CheckSystemZBuiltinFunctionCall(unsigned BuiltinID, in CheckSystemZBuiltinFunctionCall() argument
26 if (BuiltinID == SystemZ::BI__builtin_tabort) { in CheckSystemZBuiltinFunctionCall()
38 switch (BuiltinID) { in CheckSystemZBuiltinFunctionCall()
H A DSemaX86.cpp29 bool SemaX86::CheckBuiltinRoundingOrSAE(unsigned BuiltinID, CallExpr *TheCall) { in CheckBuiltinRoundingOrSAE() argument
34 switch (BuiltinID) { in CheckBuiltinRoundingOrSAE()
347 bool SemaX86::CheckBuiltinGatherScatterScale(unsigned BuiltinID, in CheckBuiltinGatherScatterScale() argument
350 switch (BuiltinID) { in CheckBuiltinGatherScatterScale()
482 bool SemaX86::CheckBuiltinTileArguments(unsigned BuiltinID, CallExpr *TheCall) { in CheckBuiltinTileArguments() argument
483 switch (BuiltinID) { in CheckBuiltinTileArguments()
532 static bool isX86_32Builtin(unsigned BuiltinID) { in isX86_32Builtin() argument
534 switch (BuiltinID) { in isX86_32Builtin()
543 bool SemaX86::CheckBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID, in CheckBuiltinFunctionCall() argument
547 if (TT.getArch() != llvm::Triple::x86 && isX86_32Builtin(BuiltinID)) in CheckBuiltinFunctionCall()
[all …]
/freebsd/contrib/llvm-project/clang/include/clang/Sema/
H A DSemaARM.h47 bool CheckARMBuiltinExclusiveCall(unsigned BuiltinID, CallExpr *TheCall,
49 bool CheckNeonBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
58 bool CheckMVEBuiltinFunctionCall(unsigned BuiltinID, CallExpr *TheCall);
59 bool CheckSVEBuiltinFunctionCall(unsigned BuiltinID, CallExpr *TheCall);
60 bool CheckSMEBuiltinFunctionCall(unsigned BuiltinID, CallExpr *TheCall);
61 bool CheckCDEBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
65 bool CheckARMBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
68 bool CheckAArch64BuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
70 bool BuiltinARMSpecialReg(unsigned BuiltinID, CallExpr *TheCall, int ArgNum,
72 bool BuiltinARMMemoryTaggingCall(unsigned BuiltinID, CallExpr *TheCall);
[all …]
H A DSemaX86.h28 bool CheckBuiltinRoundingOrSAE(unsigned BuiltinID, CallExpr *TheCall);
29 bool CheckBuiltinGatherScatterScale(unsigned BuiltinID, CallExpr *TheCall);
30 bool CheckBuiltinTileArguments(unsigned BuiltinID, CallExpr *TheCall);
35 bool CheckBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
H A DSemaMIPS.h27 bool CheckMipsBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
29 bool CheckMipsBuiltinCpu(const TargetInfo &TI, unsigned BuiltinID,
31 bool CheckMipsBuiltinArgument(unsigned BuiltinID, CallExpr *TheCall);
H A DSemaHexagon.h24 bool CheckHexagonBuiltinFunctionCall(unsigned BuiltinID, CallExpr *TheCall);
25 bool CheckHexagonBuiltinArgument(unsigned BuiltinID, CallExpr *TheCall);
H A DSemaPPC.h28 bool CheckPPCBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
43 bool BuiltinPPCMMACall(CallExpr *TheCall, unsigned BuiltinID,
H A DSemaRISCV.h37 bool CheckBuiltinFunctionCall(const TargetInfo &TI, unsigned BuiltinID,
45 bool isAliasValid(unsigned BuiltinID, llvm::StringRef AliasName);
/freebsd/contrib/llvm-project/clang/lib/CodeGen/TargetBuiltins/
H A DNVPTX.cpp35 static NVPTXMmaLdstInfo getNVPTXMmaLdstInfo(unsigned BuiltinID) { in getNVPTXMmaLdstInfo() argument
36 switch (BuiltinID) { in getNVPTXMmaLdstInfo()
210 static NVPTXMmaInfo getNVPTXMmaInfo(unsigned BuiltinID) { in getNVPTXMmaInfo() argument
253 switch (BuiltinID) { in getNVPTXMmaInfo()
378 static Value *MakeHalfType(unsigned IntrinsicID, unsigned BuiltinID, in MakeHalfType() argument
383 CGF.CGM.Error(E->getExprLoc(), C.BuiltinInfo.getQuotedName(BuiltinID) + in MakeHalfType()
388 if (BuiltinID == NVPTX::BI__nvvm_ldg_h || BuiltinID == NVPTX::BI__nvvm_ldg_h2) in MakeHalfType()
399 C.GetBuiltinType(BuiltinID, Error, &ICEArguments); in MakeHalfType()
414 Value *CodeGenFunction::EmitNVPTXBuiltinExpr(unsigned BuiltinID, in EmitNVPTXBuiltinExpr() argument
416 switch (BuiltinID) { in EmitNVPTXBuiltinExpr()
[all …]
H A DARM.cpp31 translateAarch64ToMsvcIntrin(unsigned BuiltinID) { in translateAarch64ToMsvcIntrin() argument
33 switch (BuiltinID) { in translateAarch64ToMsvcIntrin()
190 translateArmToMsvcIntrin(unsigned BuiltinID) { in translateArmToMsvcIntrin() argument
192 switch (BuiltinID) { in translateArmToMsvcIntrin()
567 unsigned BuiltinID; member
573 return BuiltinID < RHSBuiltinID; in operator <()
576 return BuiltinID < TE.BuiltinID; in operator <()
1621 unsigned BuiltinID, bool &MapProvenSorted) { in findARMVectorIntrinsicInMap() argument
1631 llvm::lower_bound(IntrinsicMap, BuiltinID); in findARMVectorIntrinsicInMap()
1633 if (Builtin != IntrinsicMap.end() && Builtin->BuiltinID == BuiltinID) in findARMVectorIntrinsicInMap()
[all …]
H A DPPC.cpp24 unsigned BuiltinID, in emitPPCLoadReserveIntrinsic() argument
32 switch (BuiltinID) { in emitPPCLoadReserveIntrinsic()
73 Value *CodeGenFunction::EmitPPCBuiltinExpr(unsigned BuiltinID, in EmitPPCBuiltinExpr() argument
140 switch (BuiltinID) { in EmitPPCBuiltinExpr()
245 if (!(BuiltinID == PPC::BI__builtin_vsx_lxvl || in EmitPPCBuiltinExpr()
246 BuiltinID == PPC::BI__builtin_vsx_lxvll)) { in EmitPPCBuiltinExpr()
251 switch (BuiltinID) { in EmitPPCBuiltinExpr()
314 if (!(BuiltinID == PPC::BI__builtin_vsx_stxvl || in EmitPPCBuiltinExpr()
315 BuiltinID == PPC::BI__builtin_vsx_stxvll)) { in EmitPPCBuiltinExpr()
320 switch (BuiltinID) { in EmitPPCBuiltinExpr()
[all …]
H A DHexagon.cpp22 getIntrinsicForHexagonNonClangBuiltin(unsigned BuiltinID) { in getIntrinsicForHexagonNonClangBuiltin() argument
24 unsigned BuiltinID; in getIntrinsicForHexagonNonClangBuiltin() member
66 auto CmpInfo = [] (Info A, Info B) { return A.BuiltinID < B.BuiltinID; }; in getIntrinsicForHexagonNonClangBuiltin()
70 const Info *F = llvm::lower_bound(Infos, Info{BuiltinID, 0, 0}, CmpInfo); in getIntrinsicForHexagonNonClangBuiltin()
71 if (F == std::end(Infos) || F->BuiltinID != BuiltinID) in getIntrinsicForHexagonNonClangBuiltin()
77 Value *CodeGenFunction::EmitHexagonBuiltinExpr(unsigned BuiltinID, in EmitHexagonBuiltinExpr() argument
81 std::tie(ID, VecLen) = getIntrinsicForHexagonNonClangBuiltin(BuiltinID); in EmitHexagonBuiltinExpr()
162 switch (BuiltinID) { in EmitHexagonBuiltinExpr()
H A DAMDGPU.cpp298 Value *CodeGenFunction::EmitAMDGPUBuiltinExpr(unsigned BuiltinID, in EmitAMDGPUBuiltinExpr() argument
302 switch (BuiltinID) { in EmitAMDGPUBuiltinExpr()
352 getContext().GetBuiltinType(BuiltinID, Error, &ICEArguments); in EmitAMDGPUBuiltinExpr()
359 CGM.getIntrinsic(BuiltinID == AMDGPU::BI__builtin_amdgcn_mov_dpp8 in EmitAMDGPUBuiltinExpr()
365 bool InsertOld = BuiltinID == AMDGPU::BI__builtin_amdgcn_mov_dpp; in EmitAMDGPUBuiltinExpr()
370 if (I < (BuiltinID == AMDGPU::BI__builtin_amdgcn_update_dpp ? 2u : 1u) && in EmitAMDGPUBuiltinExpr()
391 BuiltinID == AMDGPU::BI__builtin_amdgcn_permlane16 in EmitAMDGPUBuiltinExpr()
537 Intrinsic::ID Intrin = BuiltinID == AMDGPU::BI__builtin_amdgcn_ds_append ? in EmitAMDGPUBuiltinExpr()
570 switch (BuiltinID) { in EmitAMDGPUBuiltinExpr()
677 switch (BuiltinID) { in EmitAMDGPUBuiltinExpr()
[all …]
H A DDirectX.cpp22 Value *CodeGenFunction::EmitDirectXBuiltinExpr(unsigned BuiltinID, in EmitDirectXBuiltinExpr() argument
24 switch (BuiltinID) { in EmitDirectXBuiltinExpr()
H A DX86.cpp24 translateX86ToMsvcIntrin(unsigned BuiltinID) { in translateX86ToMsvcIntrin() argument
26 switch (BuiltinID) { in translateX86ToMsvcIntrin()
323 ArrayRef<Value *> Ops, unsigned BuiltinID, in EmitX86FMAExpr() argument
328 switch (BuiltinID) { in EmitX86FMAExpr()
408 switch (BuiltinID) { in EmitX86FMAExpr()
737 Value *CodeGenFunction::EmitX86BuiltinExpr(unsigned BuiltinID, in EmitX86BuiltinExpr() argument
739 if (BuiltinID == Builtin::BI__builtin_cpu_is) in EmitX86BuiltinExpr()
741 if (BuiltinID == Builtin::BI__builtin_cpu_supports) in EmitX86BuiltinExpr()
743 if (BuiltinID == Builtin::BI__builtin_cpu_init) in EmitX86BuiltinExpr()
748 if (std::optional<MSVCIntrin> MsvcIntId = translateX86ToMsvcIntrin(BuiltinID)) in EmitX86BuiltinExpr()
[all …]
H A DWebAssembly.cpp21 Value *CodeGenFunction::EmitWebAssemblyBuiltinExpr(unsigned BuiltinID, in EmitWebAssemblyBuiltinExpr() argument
23 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
180 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
257 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
293 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
340 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
360 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
401 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
442 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
463 switch (BuiltinID) { in EmitWebAssemblyBuiltinExpr()
/freebsd/contrib/llvm-project/clang/lib/CodeGen/
H A DCGBuiltin.cpp48 static bool shouldEmitBuiltinAsIR(unsigned BuiltinID, in shouldEmitBuiltinAsIR() argument
55 switch (BuiltinID) { in shouldEmitBuiltinAsIR()
73 unsigned BuiltinID, const CallExpr *E, in EmitTargetArchBuiltinExpr() argument
91 return CGF->EmitARMBuiltinExpr(BuiltinID, E, ReturnValue, Arch); in EmitTargetArchBuiltinExpr()
95 return CGF->EmitAArch64BuiltinExpr(BuiltinID, E, Arch); in EmitTargetArchBuiltinExpr()
98 return CGF->EmitBPFBuiltinExpr(BuiltinID, E); in EmitTargetArchBuiltinExpr()
100 return CGF->EmitDirectXBuiltinExpr(BuiltinID, E); in EmitTargetArchBuiltinExpr()
103 return CGF->EmitX86BuiltinExpr(BuiltinID, E); in EmitTargetArchBuiltinExpr()
108 return CGF->EmitPPCBuiltinExpr(BuiltinID, E); in EmitTargetArchBuiltinExpr()
111 return CGF->EmitAMDGPUBuiltinExpr(BuiltinID, E); in EmitTargetArchBuiltinExpr()
[all …]
/freebsd/contrib/llvm-project/clang/lib/AST/ByteCode/
H A DInterpBuiltin.cpp961 unsigned BuiltinID) { in interp__builtin_ctz() argument
963 if (BuiltinID == Builtin::BI__builtin_ctzg && Call->getNumArgs() == 2) { in interp__builtin_ctz()
1697 unsigned BuiltinID) { in interp__builtin_elementwise_popcount() argument
1703 if (BuiltinID == Builtin::BI__builtin_elementwise_popcount) { in interp__builtin_elementwise_popcount()
1726 if (BuiltinID == Builtin::BI__builtin_elementwise_popcount) { in interp__builtin_elementwise_popcount()
2257 unsigned BuiltinID) { in interp__builtin_elementwise_sat() argument
2269 if (BuiltinID == Builtin::BI__builtin_elementwise_add_sat) { in interp__builtin_elementwise_sat()
2271 } else if (BuiltinID == Builtin::BI__builtin_elementwise_sub_sat) { in interp__builtin_elementwise_sat()
2305 if (BuiltinID == Builtin::BI__builtin_elementwise_add_sat) { in interp__builtin_elementwise_sat()
2309 } else if (BuiltinID == Builtin::BI__builtin_elementwise_sub_sat) { in interp__builtin_elementwise_sat()
[all …]

123