| /freebsd/contrib/llvm-project/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()
|
| /freebsd/contrib/llvm-project/llvm/utils/TableGen/Common/GlobalISel/ |
| H A D | PatternParser.cpp | 133 const CodeGenIntrinsic *Intrin = getCodeGenIntrinsic(TheDef); in parseInstructionPattern() local
134 const CodeGenInstruction &Instr = getInstrForIntrinsic(CGT, Intrin); in parseInstructionPattern()
137 cast<CodeGenInstructionPattern>(*Pat).setIntrinsic(Intrin); in parseInstructionPattern()
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/NVPTX/ |
| H A D | NVPTXIntrinsics.td | 305 multiclass REDUX_SYNC<string BinOp, string PTXType, Intrinsic Intrin> {
308 [(set Int32Regs:$dst, (Intrin Int32Regs:$src, Int32Regs:$mask))]>,
342 multiclass CP_ASYNC_MBARRIER_ARRIVE<string NoInc, string AddrSpace, Intrinsic Intrin> {
345 [(Intrin Int32Regs:$addr)]>,
349 [(Intrin Int64Regs:$addr)]>,
362 multiclass CP_ASYNC_SHARED_GLOBAL_I<string cc, string cpsize, Intrinsic Intrin, Intrinsic IntrinS> {
365 [(Intrin Int32Regs:$dst, Int32Regs:$src)]>,
369 [(Intrin Int64Regs:$dst, Int64Regs:$src)]>,
440 multiclass MBARRIER_INIT<string AddrSpace, Intrinsic Intrin> {
443 [(Intrin Int32Regs:$addr, Int32Regs:$count)]>,
[all …]
|
| H A D | NVPTXISelLowering.cpp | 6199 SDValue Intrin = N->getOperand(1); in ReplaceINTRINSIC_W_CHAIN() local
6203 unsigned IntrinNo = Intrin.getNode()->getAsZExtVal(); in ReplaceINTRINSIC_W_CHAIN()
|
| /freebsd/contrib/llvm-project/llvm/lib/IR/ |
| H A D | AutoUpgrade.cpp | 1719 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86BinaryIntrinsics() local
1720 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1}); in upgradeX86BinaryIntrinsics()
1746 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86Rotate() local
1747 Value *Res = Builder.CreateCall(Intrin, {Src, Src, Amt}); in upgradeX86Rotate()
1816 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86ConcatShift() local
1817 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1, Amt}); in upgradeX86ConcatShift()
1970 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID); in upgradeX86MaskedShift() local
1971 Value *Rep = Builder.CreateCall(Intrin, in upgradeX86MaskedShift()
|
| /freebsd/contrib/llvm-project/llvm/lib/Transforms/Utils/ |
| H A D | Local.cpp | 4067 Intrinsic::ID Intrin; in recognizeBSwapOrBitReverseIdiom() local
4069 Intrin = Intrinsic::bswap; in recognizeBSwapOrBitReverseIdiom()
4071 Intrin = Intrinsic::bitreverse; in recognizeBSwapOrBitReverseIdiom()
4075 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, DemandedTy); in recognizeBSwapOrBitReverseIdiom()
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/AMDGPU/ |
| H A D | AMDGPUCodeGenPrepare.cpp | 2090 auto *Intrin = B.CreateIntrinsic( in visitAddrSpaceCastInst() local
2092 I.replaceAllUsesWith(Intrin); in visitAddrSpaceCastInst()
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/PowerPC/ |
| H A D | PPCISelLowering.cpp | 10575 static bool getVectorCompareInfo(SDValue Intrin, int &CompareOpc, in getVectorCompareInfo() argument
10577 unsigned IntrinsicID = Intrin.getConstantOperandVal(0); in getVectorCompareInfo()
15255 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXLoadForLE() local
15256 Chain = Intrin->getChain(); in expandVSXLoadForLE()
15259 Base = Intrin->getOperand(2); in expandVSXLoadForLE()
15260 MMO = Intrin->getMemOperand(); in expandVSXLoadForLE()
15323 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXStoreForLE() local
15324 Chain = Intrin->getChain(); in expandVSXStoreForLE()
15326 Base = Intrin->getOperand(3); in expandVSXStoreForLE()
15327 MMO = Intrin->getMemOperand(); in expandVSXStoreForLE()
[all …]
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/WebAssembly/ |
| H A D | WebAssemblyISelLowering.cpp | 2855 int Intrin = isNullConstant(RHS) ? Intrinsic::wasm_anytrue in performSETCCCombine() local
2864 {DAG.getConstant(Intrin, DL, MVT::i32), in performSETCCCombine()
|
| /freebsd/contrib/llvm-project/llvm/lib/Transforms/Instrumentation/ |
| H A D | MemorySanitizer.cpp | 2859 Function *Intrin = Intrinsic::getDeclaration( in handleFunnelShift() local
2861 Value *Shift = IRB.CreateCall(Intrin, {S0, S1, V2}); in handleFunnelShift()
|
| /freebsd/contrib/llvm-project/clang/lib/CodeGen/ |
| H A D | CGBuiltin.cpp | 13199 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
13200 return EmitNeonCall(Intrin, Ops, "vsri_n"); in EmitAArch64BuiltinExpr()
13205 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
13206 return EmitNeonCall(Intrin, Ops, "vsli_n"); in EmitAArch64BuiltinExpr()
18735 Intrinsic::ID Intrin = BuiltinID == AMDGPU::BI__builtin_amdgcn_ds_append ? in EmitAMDGPUBuiltinExpr() local
18738 Function *F = CGM.getIntrinsic(Intrin, { Src0->getType() }); in EmitAMDGPUBuiltinExpr()
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/X86/ |
| H A D | X86ISelLowering.cpp | 43757 SDValue Intrin = DAG.getTargetConstant( in createMMXBuildVector() local
43760 Ops[i / 2] = DAG.getNode(ISD::INTRINSIC_WO_CHAIN, DL, MVT::x86mmx, Intrin, in createMMXBuildVector()
|