| /freebsd/contrib/llvm-project/llvm/lib/Transforms/Coroutines/ |
| H A D | CoroEarly.cpp | 30 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/lib/Target/DirectX/ |
| H A D | DXILCBufferAccess.cpp | 128 CBufferRowIntrin Intrin(DL, Ty->getScalarType()); in loadValue() local
132 (TargetOffset % hlsl::CBufferRowSizeInBytes) / Intrin.EltSize; in loadValue()
135 Intrin.RetTy, Intrin.IID, in loadValue()
143 ((DL.getTypeSizeInBits(Ty) / 8) / Intrin.EltSize) - 1; in loadValue()
162 CurrentIndex %= Intrin.NumElts; in loadValue()
166 Intrin.RetTy, Intrin.IID, in loadValue()
|
| H A D | DXILOpLowering.cpp | 86 Error replaceNamedStructUses(CallInst *Intrin, CallInst *DXILOp) { in replaceNamedStructUses() argument
87 auto *IntrinTy = cast<StructType>(Intrin->getType()); in replaceNamedStructUses()
94 for (Use &U : make_early_inc_range(Intrin->uses())) in replaceNamedStructUses()
328 Error replaceResRetUses(CallInst *Intrin, CallInst *Op, bool HasCheckBit) { in replaceResRetUses() argument
331 Instruction *OldResult = Intrin; in replaceResRetUses()
332 Type *OldTy = Intrin->getType(); in replaceResRetUses()
380 if (OldResult != Intrin) { in replaceResRetUses()
381 assert(Intrin->use_empty() && "Intrinsic still has uses?"); in replaceResRetUses()
382 Intrin->eraseFromParent(); in replaceResRetUses()
452 if (OldResult != Intrin) { in replaceResRetUses()
[all …]
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/SPIRV/ |
| H A D | SPIRVLegalizePointerCast.cpp | 293 if (IntrinsicInst *Intrin = dyn_cast<IntrinsicInst>(User)) { in legalizePointerCast() local
294 if (Intrin->getIntrinsicID() == Intrinsic::spv_assign_ptr_type) { in legalizePointerCast()
295 DeadInstructions.push_back(Intrin); in legalizePointerCast()
299 if (Intrin->getIntrinsicID() == Intrinsic::spv_gep) { in legalizePointerCast()
305 if (Intrin->getIntrinsicID() == Intrinsic::spv_store) { in legalizePointerCast()
307 if (ConstantInt *C = dyn_cast<ConstantInt>(Intrin->getOperand(3))) in legalizePointerCast()
309 transformStore(B, Intrin, Intrin->getArgOperand(0), OriginalOperand, in legalizePointerCast()
|
| /freebsd/contrib/llvm-project/llvm/utils/TableGen/Common/GlobalISel/ |
| H A D | PatternParser.cpp | 121 const CodeGenIntrinsic *Intrin = &CGT.getIntrinsic(TheDef); in parseInstructionPattern() local
122 const CodeGenInstruction &Instr = getInstrForIntrinsic(CGT, Intrin); in parseInstructionPattern()
125 cast<CodeGenInstructionPattern>(*Pat).setIntrinsic(Intrin); in parseInstructionPattern()
|
| /freebsd/contrib/llvm-project/llvm/lib/CodeGen/ |
| H A D | PreISelIntrinsicLowering.cpp | 80 template <class T> static bool forEachCall(Function &Intrin, T Callback) { in forEachCall() argument
88 while (!Intrin.use_empty() && (!LastUse || LastUse->getNext())) { in forEachCall()
89 Use *U = LastUse ? LastUse->getNext() : &*Intrin.use_begin(); in forEachCall()
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/NVPTX/ |
| H A D | NVPTXIntrinsics.td | 304 multiclass REDUX_SYNC<string BinOp, string PTXType, Intrinsic Intrin> {
307 [(set i32:$dst, (Intrin i32:$src, B32:$mask))]>,
402 multiclass CP_ASYNC_MBARRIER_ARRIVE<string NoInc, string AddrSpace, Intrinsic Intrin> {
405 [(Intrin addr:$addr)]>,
418 multiclass CP_ASYNC_SHARED_GLOBAL_I<string cc, string cpsize, Intrinsic Intrin, Intrinsic IntrinS> {
421 [(Intrin addr:$dst, addr:$src)]>,
845 multiclass MBARRIER_INIT<string AddrSpace, Intrinsic Intrin> {
848 [(Intrin addr:$addr, i32:$count)]>,
856 multiclass MBARRIER_INVAL<string AddrSpace, Intrinsic Intrin> {
859 [(Intrin addr:$addr)]>,
[all …]
|
| H A D | NVPTXISelLowering.cpp | 2643 SDValue Intrin = N->getOperand(1); in LowerIntrinsicVoid() local
2646 unsigned IntrinNo = cast<ConstantSDNode>(Intrin.getNode())->getZExtValue(); in LowerIntrinsicVoid()
6004 SDValue Intrin = N->getOperand(1); in ReplaceINTRINSIC_W_CHAIN() local
6008 unsigned IntrinNo = Intrin.getNode()->getAsZExtVal(); in ReplaceINTRINSIC_W_CHAIN()
|
| /freebsd/contrib/llvm-project/clang/lib/CodeGen/TargetBuiltins/ |
| H A D | AMDGPU.cpp | 537 Intrinsic::ID Intrin = BuiltinID == AMDGPU::BI__builtin_amdgcn_ds_append ? in EmitAMDGPUBuiltinExpr() local
540 Function *F = CGM.getIntrinsic(Intrin, { Src0->getType() }); in EmitAMDGPUBuiltinExpr()
|
| H A D | ARM.cpp | 7403 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
7404 return EmitNeonCall(Intrin, Ops, "vsri_n"); in EmitAArch64BuiltinExpr()
7409 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
7410 return EmitNeonCall(Intrin, Ops, "vsli_n"); in EmitAArch64BuiltinExpr()
|
| /freebsd/contrib/llvm-project/llvm/lib/Transforms/Utils/ |
| H A D | Local.cpp | 4160 Intrinsic::ID Intrin; in recognizeBSwapOrBitReverseIdiom() local
4162 Intrin = Intrinsic::bswap; in recognizeBSwapOrBitReverseIdiom()
4164 Intrin = Intrinsic::bitreverse; in recognizeBSwapOrBitReverseIdiom()
4169 Intrinsic::getOrInsertDeclaration(I->getModule(), Intrin, DemandedTy); in recognizeBSwapOrBitReverseIdiom()
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/AMDGPU/ |
| H A D | AMDGPUCodeGenPrepare.cpp | 2190 auto *Intrin = B.CreateIntrinsic( in visitAddrSpaceCastInst() local
2192 I.replaceAllUsesWith(Intrin); in visitAddrSpaceCastInst()
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/PowerPC/ |
| H A D | PPCISelLowering.cpp | 10822 static bool getVectorCompareInfo(SDValue Intrin, int &CompareOpc, in getVectorCompareInfo() argument
10824 unsigned IntrinsicID = Intrin.getConstantOperandVal(0); in getVectorCompareInfo()
16088 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXLoadForLE() local
16089 Chain = Intrin->getChain(); in expandVSXLoadForLE()
16092 Base = Intrin->getOperand(2); in expandVSXLoadForLE()
16093 MMO = Intrin->getMemOperand(); in expandVSXLoadForLE()
16156 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXStoreForLE() local
16157 Chain = Intrin->getChain(); in expandVSXStoreForLE()
16159 Base = Intrin->getOperand(3); in expandVSXStoreForLE()
16160 MMO = Intrin->getMemOperand(); in expandVSXStoreForLE()
[all …]
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/WebAssembly/ |
| H A D | WebAssemblyISelLowering.cpp | 3340 Intrinsic::ID Intrin>
3354 {DAG.getConstant(Intrin, DL, MVT::i32), in TryMatchTrue()
|
| /freebsd/contrib/llvm-project/llvm/lib/Target/X86/ |
| H A D | X86ISelLowering.cpp | 45590 SDValue Intrin = DAG.getTargetConstant( in createMMXBuildVector() local
45593 Ops[i / 2] = DAG.getNode(ISD::INTRINSIC_WO_CHAIN, DL, MVT::x86mmx, Intrin, in createMMXBuildVector()
|