| /netbsd-src/external/apache2/llvm/dist/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()
|
| /netbsd-src/external/apache2/llvm/dist/llvm/lib/Target/AMDGPU/ |
| H A D | AMDGPUUnifyDivergentExitNodes.cpp | 140 if (IntrinsicInst *Intrin = llvm::dyn_cast<IntrinsicInst>(&I)) { in removeDoneExport() local
141 if (Intrin->getIntrinsicID() == Intrinsic::amdgcn_exp) { in removeDoneExport()
142 Intrin->setArgOperand(6, BoolFalse); // done in removeDoneExport()
143 } else if (Intrin->getIntrinsicID() == Intrinsic::amdgcn_exp_compr) { in removeDoneExport()
144 Intrin->setArgOperand(4, BoolFalse); // done in removeDoneExport()
|
| H A D | AMDGPUCodeGenPrepare.cpp | 526 FunctionCallee Intrin = Intrinsic::getDeclaration(Mod, IntrID); in replaceMulWithMul24() local
537 Value *Result = Builder.CreateCall(Intrin, {LHS, RHS}); in replaceMulWithMul24()
|
| /netbsd-src/external/apache2/llvm/dist/llvm/lib/Target/NVPTX/ |
| H A D | NVPTXIntrinsics.td | 277 multiclass REDUX_SYNC<string BinOp, string PTXType, Intrinsic Intrin> {
280 [(set Int32Regs:$dst, (Intrin Int32Regs:$src, Int32Regs:$mask))]>,
311 multiclass CP_ASYNC_MBARRIER_ARRIVE<string NoInc, string AddrSpace, Intrinsic Intrin> {
314 [(Intrin Int32Regs:$addr)]>,
318 [(Intrin Int64Regs:$addr)]>,
331 multiclass CP_ASYNC_CA_SHARED_GLOBAL_I<string cpsize, Intrinsic Intrin> {
334 [(Intrin Int32Regs:$dst, Int32Regs:$src)]>,
338 [(Intrin Int64Regs:$dst, Int64Regs:$src)]>,
351 multiclass CP_ASYNC_CG_SHARED_GLOBAL<string cpsize, Intrinsic Intrin> {
354 [(Intrin Int32Regs:$dst, Int32Regs:$src)]>,
[all …]
|
| H A D | NVPTXISelLowering.cpp | 4884 SDValue Intrin = N->getOperand(1); in ReplaceINTRINSIC_W_CHAIN() local
4888 unsigned IntrinNo = cast<ConstantSDNode>(Intrin.getNode())->getZExtValue(); in ReplaceINTRINSIC_W_CHAIN()
|
| /netbsd-src/external/apache2/llvm/dist/llvm/lib/IR/ |
| H A D | AutoUpgrade.cpp | 1267 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in UpgradeX86BinaryIntrinsics() local
1268 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1}); in UpgradeX86BinaryIntrinsics()
1294 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86Rotate() local
1295 Value *Res = Builder.CreateCall(Intrin, {Src, Src, Amt}); in upgradeX86Rotate()
1364 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86ConcatShift() local
1365 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1, Amt}); in upgradeX86ConcatShift()
1520 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID); in UpgradeX86MaskedShift() local
1521 Value *Rep = Builder.CreateCall(Intrin, in UpgradeX86MaskedShift()
|
| /netbsd-src/external/apache2/llvm/dist/llvm/lib/Transforms/Utils/ |
| H A D | Local.cpp | 3180 Intrinsic::ID Intrin; in recognizeBSwapOrBitReverseIdiom() local
3182 Intrin = Intrinsic::bswap; in recognizeBSwapOrBitReverseIdiom()
3184 Intrin = Intrinsic::bitreverse; in recognizeBSwapOrBitReverseIdiom()
3188 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, DemandedTy); in recognizeBSwapOrBitReverseIdiom()
|
| /netbsd-src/external/apache2/llvm/dist/llvm/lib/Target/PowerPC/ |
| H A D | PPCISelLowering.cpp | 10008 static bool getVectorCompareInfo(SDValue Intrin, int &CompareOpc, in getVectorCompareInfo() argument
10011 cast<ConstantSDNode>(Intrin.getOperand(0))->getZExtValue(); in getVectorCompareInfo()
14172 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXLoadForLE() local
14173 Chain = Intrin->getChain(); in expandVSXLoadForLE()
14176 Base = Intrin->getOperand(2); in expandVSXLoadForLE()
14177 MMO = Intrin->getMemOperand(); in expandVSXLoadForLE()
14242 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXStoreForLE() local
14243 Chain = Intrin->getChain(); in expandVSXStoreForLE()
14245 Base = Intrin->getOperand(3); in expandVSXStoreForLE()
14246 MMO = Intrin->getMemOperand(); in expandVSXStoreForLE()
|
| /netbsd-src/external/apache2/llvm/dist/clang/lib/CodeGen/ |
| H A D | CGBuiltin.cpp | 11226 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
11227 return EmitNeonCall(Intrin, Ops, "vsri_n"); in EmitAArch64BuiltinExpr()
11232 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
11233 return EmitNeonCall(Intrin, Ops, "vsli_n"); in EmitAArch64BuiltinExpr()
15678 Intrinsic::ID Intrin = BuiltinID == AMDGPU::BI__builtin_amdgcn_ds_append ? in EmitAMDGPUBuiltinExpr() local
15681 Function *F = CGM.getIntrinsic(Intrin, { Src0->getType() }); in EmitAMDGPUBuiltinExpr()
15687 Intrinsic::ID Intrin; in EmitAMDGPUBuiltinExpr() local
15690 Intrin = Intrinsic::amdgcn_ds_fadd; in EmitAMDGPUBuiltinExpr()
15693 Intrin = Intrinsic::amdgcn_ds_fmin; in EmitAMDGPUBuiltinExpr()
15696 Intrin = Intrinsic::amdgcn_ds_fmax; in EmitAMDGPUBuiltinExpr()
[all …]
|
| /netbsd-src/external/apache2/llvm/dist/llvm/lib/Transforms/InstCombine/ |
| H A D | InstCombineCompares.cpp | 1037 } else if (const auto *Intrin = dyn_cast<IntrinsicInst>(V)) { in foldAllocaCmp() local
1038 switch (Intrin->getIntrinsicID()) { in foldAllocaCmp()
|
| /netbsd-src/external/apache2/llvm/dist/llvm/lib/Target/X86/ |
| H A D | X86ISelLowering.cpp | 39831 SDValue Intrin = DAG.getTargetConstant( in createMMXBuildVector() local
39834 Ops[i / 2] = DAG.getNode(ISD::INTRINSIC_WO_CHAIN, DL, MVT::x86mmx, Intrin, in createMMXBuildVector()
|