| /freebsd-13.1/contrib/llvm-project/llvm/lib/Transforms/Coroutines/ |
| H A D | CoroEarly.cpp | 28 void lowerCoroPromise(CoroPromiseInst *Intrin);
60 void Lowerer::lowerCoroPromise(CoroPromiseInst *Intrin) { in lowerCoroPromise() argument
61 Value *Operand = Intrin->getArgOperand(0); in lowerCoroPromise()
62 Align Alignment = Intrin->getAlignment(); in lowerCoroPromise()
70 if (Intrin->isFromPromise()) in lowerCoroPromise()
73 Builder.SetInsertPoint(Intrin); in lowerCoroPromise()
77 Intrin->replaceAllUsesWith(Replacement); in lowerCoroPromise()
78 Intrin->eraseFromParent(); in lowerCoroPromise()
|
| /freebsd-13.1/contrib/llvm-project/llvm/lib/Target/NVPTX/ |
| H A D | NVPTXIntrinsics.td | 314 [(Intrin Int32Regs:$addr)]>,
318 [(Intrin Int64Regs:$addr)]>,
334 [(Intrin Int32Regs:$dst, Int32Regs:$src)]>,
338 [(Intrin Int64Regs:$dst, Int64Regs:$src)]>,
386 [(Intrin Int32Regs:$addr, Int32Regs:$count)]>,
390 [(Intrin Int64Regs:$addr, Int32Regs:$count)]>,
401 [(Intrin Int32Regs:$addr)]>,
405 [(Intrin Int64Regs:$addr)]>,
503 class MBARRIER_PENDING_COUNT<Intrinsic Intrin> :
2116 multiclass NG_TO_G<string Str, Intrinsic Intrin> {
[all …]
|
| H A D | NVPTXISelLowering.cpp | 4970 SDValue Intrin = N->getOperand(1); in ReplaceINTRINSIC_W_CHAIN() local
4974 unsigned IntrinNo = cast<ConstantSDNode>(Intrin.getNode())->getZExtValue(); in ReplaceINTRINSIC_W_CHAIN()
|
| /freebsd-13.1/contrib/llvm-project/llvm/lib/IR/ |
| H A D | AutoUpgrade.cpp | 1273 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in UpgradeX86BinaryIntrinsics() local
1274 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1}); in UpgradeX86BinaryIntrinsics()
1300 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86Rotate() local
1301 Value *Res = Builder.CreateCall(Intrin, {Src, Src, Amt}); in upgradeX86Rotate()
1370 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86ConcatShift() local
1371 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1, Amt}); in upgradeX86ConcatShift()
1525 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID); in UpgradeX86MaskedShift() local
1526 Value *Rep = Builder.CreateCall(Intrin, in UpgradeX86MaskedShift()
|
| /freebsd-13.1/contrib/llvm-project/llvm/lib/Target/AMDGPU/ |
| H A D | AMDGPUCodeGenPrepare.cpp | 528 FunctionCallee Intrin = Intrinsic::getDeclaration(Mod, IntrID); in replaceMulWithMul24() local
539 Value *Result = Builder.CreateCall(Intrin, {LHS, RHS}); in replaceMulWithMul24()
|
| /freebsd-13.1/contrib/llvm-project/llvm/lib/Transforms/Utils/ |
| H A D | Local.cpp | 3189 Intrinsic::ID Intrin; in recognizeBSwapOrBitReverseIdiom() local
3191 Intrin = Intrinsic::bswap; in recognizeBSwapOrBitReverseIdiom()
3193 Intrin = Intrinsic::bitreverse; in recognizeBSwapOrBitReverseIdiom()
3197 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, DemandedTy); in recognizeBSwapOrBitReverseIdiom()
|
| /freebsd-13.1/contrib/llvm-project/clang/lib/CodeGen/ |
| H A D | CGBuiltin.cpp | 11331 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
11332 return EmitNeonCall(Intrin, Ops, "vsri_n"); in EmitAArch64BuiltinExpr()
11337 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
11338 return EmitNeonCall(Intrin, Ops, "vsli_n"); in EmitAArch64BuiltinExpr()
16191 Intrinsic::ID Intrin = BuiltinID == AMDGPU::BI__builtin_amdgcn_ds_append ? in EmitAMDGPUBuiltinExpr() local
16194 Function *F = CGM.getIntrinsic(Intrin, { Src0->getType() }); in EmitAMDGPUBuiltinExpr()
16200 Intrinsic::ID Intrin; in EmitAMDGPUBuiltinExpr() local
16203 Intrin = Intrinsic::amdgcn_ds_fadd; in EmitAMDGPUBuiltinExpr()
16206 Intrin = Intrinsic::amdgcn_ds_fmin; in EmitAMDGPUBuiltinExpr()
16209 Intrin = Intrinsic::amdgcn_ds_fmax; in EmitAMDGPUBuiltinExpr()
[all …]
|
| /freebsd-13.1/contrib/llvm-project/llvm/lib/Target/PowerPC/ |
| H A D | PPCISelLowering.cpp | 10052 static bool getVectorCompareInfo(SDValue Intrin, int &CompareOpc, in getVectorCompareInfo() argument
10055 cast<ConstantSDNode>(Intrin.getOperand(0))->getZExtValue(); in getVectorCompareInfo()
14227 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXLoadForLE() local
14228 Chain = Intrin->getChain(); in expandVSXLoadForLE()
14231 Base = Intrin->getOperand(2); in expandVSXLoadForLE()
14232 MMO = Intrin->getMemOperand(); in expandVSXLoadForLE()
14297 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXStoreForLE() local
14298 Chain = Intrin->getChain(); in expandVSXStoreForLE()
14300 Base = Intrin->getOperand(3); in expandVSXStoreForLE()
14301 MMO = Intrin->getMemOperand(); in expandVSXStoreForLE()
|
| /freebsd-13.1/contrib/llvm-project/llvm/lib/Transforms/Instrumentation/ |
| H A D | MemorySanitizer.cpp | 2533 Function *Intrin = Intrinsic::getDeclaration( in handleFunnelShift() local
2535 Value *Shift = IRB.CreateCall(Intrin, {S0, S1, V2}); in handleFunnelShift()
|
| /freebsd-13.1/contrib/llvm-project/llvm/lib/Transforms/InstCombine/ |
| H A D | InstCombineCompares.cpp | 1060 } else if (const auto *Intrin = dyn_cast<IntrinsicInst>(V)) { in foldAllocaCmp() local
1061 switch (Intrin->getIntrinsicID()) { in foldAllocaCmp()
|
| /freebsd-13.1/contrib/llvm-project/llvm/lib/Target/X86/ |
| H A D | X86ISelLowering.cpp | 40088 SDValue Intrin = DAG.getTargetConstant( in createMMXBuildVector() local
40091 Ops[i / 2] = DAG.getNode(ISD::INTRINSIC_WO_CHAIN, DL, MVT::x86mmx, Intrin, in createMMXBuildVector()
|