| /openbsd-src/gnu/llvm/llvm/lib/Transforms/Coroutines/ |
| H A D | CoroEarly.cpp | 29 void lowerCoroPromise(CoroPromiseInst *Intrin);
61 void Lowerer::lowerCoroPromise(CoroPromiseInst *Intrin) { in lowerCoroPromise() argument
62 Value *Operand = Intrin->getArgOperand(0); in lowerCoroPromise()
63 Align Alignment = Intrin->getAlignment(); in lowerCoroPromise()
71 if (Intrin->isFromPromise()) in lowerCoroPromise()
74 Builder.SetInsertPoint(Intrin); in lowerCoroPromise()
78 Intrin->replaceAllUsesWith(Replacement); in lowerCoroPromise()
79 Intrin->eraseFromParent(); in lowerCoroPromise()
|
| /openbsd-src/gnu/llvm/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 | 5229 SDValue Intrin = N->getOperand(1); in ReplaceINTRINSIC_W_CHAIN() local
5233 unsigned IntrinNo = cast<ConstantSDNode>(Intrin.getNode())->getZExtValue(); in ReplaceINTRINSIC_W_CHAIN()
|
| /openbsd-src/gnu/llvm/llvm/lib/IR/ |
| H A D | AutoUpgrade.cpp | 1478 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in UpgradeX86BinaryIntrinsics() local
1479 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1}); in UpgradeX86BinaryIntrinsics()
1505 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86Rotate() local
1506 Value *Res = Builder.CreateCall(Intrin, {Src, Src, Amt}); in upgradeX86Rotate()
1575 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86ConcatShift() local
1576 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1, Amt}); in upgradeX86ConcatShift()
1731 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID); in UpgradeX86MaskedShift() local
1732 Value *Rep = Builder.CreateCall(Intrin, in UpgradeX86MaskedShift()
|
| /openbsd-src/gnu/llvm/llvm/lib/Transforms/Utils/ |
| H A D | Local.cpp | 3332 Intrinsic::ID Intrin; in recognizeBSwapOrBitReverseIdiom() local
3334 Intrin = Intrinsic::bswap; in recognizeBSwapOrBitReverseIdiom()
3336 Intrin = Intrinsic::bitreverse; in recognizeBSwapOrBitReverseIdiom()
3340 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, DemandedTy); in recognizeBSwapOrBitReverseIdiom()
|
| /openbsd-src/gnu/llvm/llvm/lib/Target/PowerPC/ |
| H A D | PPCISelLowering.cpp | 10299 static bool getVectorCompareInfo(SDValue Intrin, int &CompareOpc, in getVectorCompareInfo() argument
10302 cast<ConstantSDNode>(Intrin.getOperand(0))->getZExtValue(); in getVectorCompareInfo()
14736 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXLoadForLE() local
14737 Chain = Intrin->getChain(); in expandVSXLoadForLE()
14740 Base = Intrin->getOperand(2); in expandVSXLoadForLE()
14741 MMO = Intrin->getMemOperand(); in expandVSXLoadForLE()
14804 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXStoreForLE() local
14805 Chain = Intrin->getChain(); in expandVSXStoreForLE()
14807 Base = Intrin->getOperand(3); in expandVSXStoreForLE()
14808 MMO = Intrin->getMemOperand(); in expandVSXStoreForLE()
[all …]
|
| /openbsd-src/gnu/llvm/clang/lib/CodeGen/ |
| H A D | CGBuiltin.cpp | 11917 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
11918 return EmitNeonCall(Intrin, Ops, "vsri_n"); in EmitAArch64BuiltinExpr()
11923 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
11924 return EmitNeonCall(Intrin, Ops, "vsli_n"); in EmitAArch64BuiltinExpr()
17026 Intrinsic::ID Intrin = BuiltinID == AMDGPU::BI__builtin_amdgcn_ds_append ? in EmitAMDGPUBuiltinExpr() local
17029 Function *F = CGM.getIntrinsic(Intrin, { Src0->getType() }); in EmitAMDGPUBuiltinExpr()
17035 Intrinsic::ID Intrin; in EmitAMDGPUBuiltinExpr() local
17038 Intrin = Intrinsic::amdgcn_ds_fadd; in EmitAMDGPUBuiltinExpr()
17041 Intrin = Intrinsic::amdgcn_ds_fmin; in EmitAMDGPUBuiltinExpr()
17044 Intrin = Intrinsic::amdgcn_ds_fmax; in EmitAMDGPUBuiltinExpr()
[all …]
|
| /openbsd-src/gnu/llvm/llvm/lib/Transforms/Instrumentation/ |
| H A D | MemorySanitizer.cpp | 2746 Function *Intrin = Intrinsic::getDeclaration( in handleFunnelShift() local
2748 Value *Shift = IRB.CreateCall(Intrin, {S0, S1, V2}); in handleFunnelShift()
|
| /openbsd-src/gnu/llvm/llvm/lib/Transforms/InstCombine/ |
| H A D | InstCombineCompares.cpp | 949 } else if (const auto *Intrin = dyn_cast<IntrinsicInst>(V)) { in foldAllocaCmp() local
950 switch (Intrin->getIntrinsicID()) { in foldAllocaCmp()
|
| /openbsd-src/gnu/llvm/llvm/lib/Target/X86/ |
| H A D | X86ISelLowering.cpp | 43722 SDValue Intrin = DAG.getTargetConstant( in createMMXBuildVector() local
43725 Ops[i / 2] = DAG.getNode(ISD::INTRINSIC_WO_CHAIN, DL, MVT::x86mmx, Intrin, in createMMXBuildVector()
|