Home
last modified time | relevance | path

Searched refs:Intrin (Results 1 – 25 of 34) sorted by relevance

12

/external/swiftshader/third_party/llvm-10.0/llvm/lib/Transforms/Coroutines/
DCoroEarly.cpp32 void lowerCoroPromise(CoroPromiseInst *Intrin);
65 void Lowerer::lowerCoroPromise(CoroPromiseInst *Intrin) { in lowerCoroPromise() argument
66 Value *Operand = Intrin->getArgOperand(0); in lowerCoroPromise()
67 unsigned Alignement = Intrin->getAlignment(); in lowerCoroPromise()
75 if (Intrin->isFromPromise()) in lowerCoroPromise()
78 Builder.SetInsertPoint(Intrin); in lowerCoroPromise()
82 Intrin->replaceAllUsesWith(Replacement); in lowerCoroPromise()
83 Intrin->eraseFromParent(); in lowerCoroPromise()
/external/llvm-project/llvm/lib/Transforms/Coroutines/
DCoroEarly.cpp28 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()
/external/swiftshader/third_party/llvm-10.0/llvm/lib/Target/AMDGPU/
DAMDGPUUnifyDivergentExitNodes.cpp125 if (IntrinsicInst *Intrin = llvm::dyn_cast<IntrinsicInst>(&I)) { in removeDoneExport() local
126 if (Intrin->getIntrinsicID() == Intrinsic::amdgcn_exp) { in removeDoneExport()
127 Intrin->setArgOperand(6, BoolFalse); // done in removeDoneExport()
128 } else if (Intrin->getIntrinsicID() == Intrinsic::amdgcn_exp_compr) { in removeDoneExport()
129 Intrin->setArgOperand(4, BoolFalse); // done in removeDoneExport()
DAMDGPUCodeGenPrepare.cpp498 FunctionCallee Intrin = Intrinsic::getDeclaration(Mod, IntrID); in replaceMulWithMul24() local
509 Value *Result = Builder.CreateCall(Intrin, {LHS, RHS}); in replaceMulWithMul24()
/external/llvm-project/llvm/lib/Target/AMDGPU/
DAMDGPUUnifyDivergentExitNodes.cpp126 if (IntrinsicInst *Intrin = llvm::dyn_cast<IntrinsicInst>(&I)) { in removeDoneExport() local
127 if (Intrin->getIntrinsicID() == Intrinsic::amdgcn_exp) { in removeDoneExport()
128 Intrin->setArgOperand(6, BoolFalse); // done in removeDoneExport()
129 } else if (Intrin->getIntrinsicID() == Intrinsic::amdgcn_exp_compr) { in removeDoneExport()
130 Intrin->setArgOperand(4, BoolFalse); // done in removeDoneExport()
DAMDGPUCodeGenPrepare.cpp548 FunctionCallee Intrin = Intrinsic::getDeclaration(Mod, IntrID); in replaceMulWithMul24() local
559 Value *Result = Builder.CreateCall(Intrin, {LHS, RHS}); in replaceMulWithMul24()
/external/llvm/lib/Target/AMDGPU/
DAMDGPUAnnotateKernelFeatures.cpp30 void addAttrToCallers(Function *Intrin, StringRef AttrName);
141 void AMDGPUAnnotateKernelFeatures::addAttrToCallers(Function *Intrin, in addAttrToCallers() argument
145 for (User *U : Intrin->users()) { in addAttrToCallers()
/external/compiler-rt/lib/profile/
DCMakeLists.txt4 #include <Intrin.h> /* Workaround for PR19898. */
/external/llvm/cmake/modules/
DCheckAtomic.cmake83 #include <Intrin.h> /* Workaround for PR19898. */
/external/llvm/lib/Transforms/Utils/
DLocal.cpp1921 Intrinsic::ID Intrin; in recognizeBSwapOrBitReverseIdiom() local
1923 Intrin = Intrinsic::bswap; in recognizeBSwapOrBitReverseIdiom()
1925 Intrin = Intrinsic::bitreverse; in recognizeBSwapOrBitReverseIdiom()
1930 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, DemandedTy); in recognizeBSwapOrBitReverseIdiom()
1947 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, ITy); in recognizeBSwapOrBitReverseIdiom()
/external/llvm-project/llvm/unittests/Transforms/Utils/
DLocalTest.cpp1022 FunctionCallee Intrin = M.getOrInsertFunction("llvm.foo", FnType); in TEST() local
1029 auto *CallToIntrin = B.CreateCall(Intrin); in TEST()
/external/swiftshader/third_party/llvm-10.0/llvm/lib/Transforms/Utils/
DLocal.cpp2872 Intrinsic::ID Intrin; in recognizeBSwapOrBitReverseIdiom() local
2874 Intrin = Intrinsic::bswap; in recognizeBSwapOrBitReverseIdiom()
2876 Intrin = Intrinsic::bitreverse; in recognizeBSwapOrBitReverseIdiom()
2881 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, DemandedTy); in recognizeBSwapOrBitReverseIdiom()
2898 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, ITy); in recognizeBSwapOrBitReverseIdiom()
/external/swiftshader/third_party/llvm-10.0/llvm/lib/IR/
DAutoUpgrade.cpp1123 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in UpgradeX86AddSubSatIntrinsics() local
1124 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1}); in UpgradeX86AddSubSatIntrinsics()
1150 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86Rotate() local
1151 Value *Res = Builder.CreateCall(Intrin, {Src, Src, Amt}); in upgradeX86Rotate()
1220 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86ConcatShift() local
1221 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1, Amt}); in upgradeX86ConcatShift()
1385 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID); in UpgradeX86MaskedShift() local
1386 Value *Rep = Builder.CreateCall(Intrin, in UpgradeX86MaskedShift()
/external/llvm-project/llvm/lib/IR/
DAutoUpgrade.cpp1241 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in UpgradeX86BinaryIntrinsics() local
1242 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1}); in UpgradeX86BinaryIntrinsics()
1268 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86Rotate() local
1269 Value *Res = Builder.CreateCall(Intrin, {Src, Src, Amt}); in upgradeX86Rotate()
1338 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID, Ty); in upgradeX86ConcatShift() local
1339 Value *Res = Builder.CreateCall(Intrin, {Op0, Op1, Amt}); in upgradeX86ConcatShift()
1494 Function *Intrin = Intrinsic::getDeclaration(CI.getModule(), IID); in UpgradeX86MaskedShift() local
1495 Value *Rep = Builder.CreateCall(Intrin, in UpgradeX86MaskedShift()
/external/llvm-project/llvm/lib/Transforms/Utils/
DLocal.cpp3095 Intrinsic::ID Intrin; in recognizeBSwapOrBitReverseIdiom() local
3097 Intrin = Intrinsic::bswap; in recognizeBSwapOrBitReverseIdiom()
3099 Intrin = Intrinsic::bitreverse; in recognizeBSwapOrBitReverseIdiom()
3103 Function *F = Intrinsic::getDeclaration(I->getModule(), Intrin, DemandedTy); in recognizeBSwapOrBitReverseIdiom()
/external/llvm/lib/Target/NVPTX/
DNVPTXIntrinsics.td1588 multiclass NG_TO_G<string Str, Intrinsic Intrin> {
1591 [(set Int32Regs:$result, (Intrin Int32Regs:$src))]>,
1595 [(set Int64Regs:$result, (Intrin Int64Regs:$src))]>,
1602 [(set Int32Regs:$result, (Intrin (Wrapper tglobaladdr:$src)))]>,
1606 [(set Int64Regs:$result, (Intrin (Wrapper tglobaladdr:$src)))]>,
1611 [(set Int32Regs:$result, (Intrin Int32Regs:$src))]>;
1614 [(set Int64Regs:$result, (Intrin Int64Regs:$src))]>;
1620 [(set Int32Regs:$result, (Intrin (Wrapper tglobaladdr:$src)))]>;
1623 [(set Int64Regs:$result, (Intrin (Wrapper tglobaladdr:$src)))]>;*/
1626 multiclass G_TO_NG<string Str, Intrinsic Intrin> {
[all …]
DNVPTXISelLowering.cpp4391 SDValue Intrin = N->getOperand(1); in ReplaceINTRINSIC_W_CHAIN() local
4395 unsigned IntrinNo = cast<ConstantSDNode>(Intrin.getNode())->getZExtValue(); in ReplaceINTRINSIC_W_CHAIN()
/external/swiftshader/third_party/subzero/src/
DIceTargetLoweringX86BaseImpl.h835 } else if (auto *Intrin = llvm::dyn_cast<InstIntrinsic>(CurInst)) {
839 Intrinsics::IntrinsicID ID = Intrin->getIntrinsicID();
841 (Traits::Is64Bit || Intrin->getDest()->getType() != IceType_i64) &&
843 ID, getConstantMemoryOrder(Intrin->getArg(1)))) {
844 LoadDest = Intrin->getDest();
846 LoadSrc = formMemoryOperand(Intrin->getArg(0), LoadDest->getType(),
/external/llvm/lib/Target/PowerPC/
DPPCISelLowering.cpp7656 static bool getVectorCompareInfo(SDValue Intrin, int &CompareOpc, in getVectorCompareInfo() argument
7659 cast<ConstantSDNode>(Intrin.getOperand(0))->getZExtValue(); in getVectorCompareInfo()
10457 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXLoadForLE() local
10458 Chain = Intrin->getChain(); in expandVSXLoadForLE()
10461 Base = Intrin->getOperand(2); in expandVSXLoadForLE()
10462 MMO = Intrin->getMemOperand(); in expandVSXLoadForLE()
10519 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXStoreForLE() local
10520 Chain = Intrin->getChain(); in expandVSXStoreForLE()
10522 Base = Intrin->getOperand(3); in expandVSXStoreForLE()
10523 MMO = Intrin->getMemOperand(); in expandVSXStoreForLE()
/external/swiftshader/third_party/llvm-10.0/llvm/lib/Target/PowerPC/
DPPCISelLowering.cpp9516 static bool getVectorCompareInfo(SDValue Intrin, int &CompareOpc, in getVectorCompareInfo() argument
9519 cast<ConstantSDNode>(Intrin.getOperand(0))->getZExtValue(); in getVectorCompareInfo()
13459 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXLoadForLE() local
13460 Chain = Intrin->getChain(); in expandVSXLoadForLE()
13463 Base = Intrin->getOperand(2); in expandVSXLoadForLE()
13464 MMO = Intrin->getMemOperand(); in expandVSXLoadForLE()
13529 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXStoreForLE() local
13530 Chain = Intrin->getChain(); in expandVSXStoreForLE()
13532 Base = Intrin->getOperand(3); in expandVSXStoreForLE()
13533 MMO = Intrin->getMemOperand(); in expandVSXStoreForLE()
/external/llvm-project/llvm/lib/Target/PowerPC/
DPPCISelLowering.cpp10276 static bool getVectorCompareInfo(SDValue Intrin, int &CompareOpc, in getVectorCompareInfo() argument
10279 cast<ConstantSDNode>(Intrin.getOperand(0))->getZExtValue(); in getVectorCompareInfo()
14321 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXLoadForLE() local
14322 Chain = Intrin->getChain(); in expandVSXLoadForLE()
14325 Base = Intrin->getOperand(2); in expandVSXLoadForLE()
14326 MMO = Intrin->getMemOperand(); in expandVSXLoadForLE()
14391 MemIntrinsicSDNode *Intrin = cast<MemIntrinsicSDNode>(N); in expandVSXStoreForLE() local
14392 Chain = Intrin->getChain(); in expandVSXStoreForLE()
14394 Base = Intrin->getOperand(3); in expandVSXStoreForLE()
14395 MMO = Intrin->getMemOperand(); in expandVSXStoreForLE()
/external/llvm-project/clang/lib/CodeGen/
DCGBuiltin.cpp10785 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
10786 return EmitNeonCall(Intrin, Ops, "vsri_n"); in EmitAArch64BuiltinExpr()
10791 llvm::Function *Intrin = CGM.getIntrinsic(Int, Ty); in EmitAArch64BuiltinExpr() local
10792 return EmitNeonCall(Intrin, Ops, "vsli_n"); in EmitAArch64BuiltinExpr()
15166 Intrinsic::ID Intrin = BuiltinID == AMDGPU::BI__builtin_amdgcn_ds_append ? in EmitAMDGPUBuiltinExpr() local
15169 Function *F = CGM.getIntrinsic(Intrin, { Src0->getType() }); in EmitAMDGPUBuiltinExpr()
15175 Intrinsic::ID Intrin; in EmitAMDGPUBuiltinExpr() local
15178 Intrin = Intrinsic::amdgcn_ds_fadd; in EmitAMDGPUBuiltinExpr()
15181 Intrin = Intrinsic::amdgcn_ds_fmin; in EmitAMDGPUBuiltinExpr()
15184 Intrin = Intrinsic::amdgcn_ds_fmax; in EmitAMDGPUBuiltinExpr()
[all …]
/external/llvm-project/llvm/lib/Target/NVPTX/
DNVPTXIntrinsics.td1895 multiclass NG_TO_G<string Str, Intrinsic Intrin> {
1898 [(set Int32Regs:$result, (Intrin Int32Regs:$src))]>;
1901 [(set Int64Regs:$result, (Intrin Int64Regs:$src))]>;
1906 [(set Int64Regs:$result, (Intrin Int32Regs:$src))]>,
1910 multiclass G_TO_NG<string Str, Intrinsic Intrin> {
1913 [(set Int32Regs:$result, (Intrin Int32Regs:$src))]>;
1916 [(set Int64Regs:$result, (Intrin Int64Regs:$src))]>;
1921 [(set Int32Regs:$result, (Intrin Int64Regs:$src))]>,
/external/swiftshader/third_party/llvm-10.0/llvm/lib/Target/NVPTX/
DNVPTXIntrinsics.td1895 multiclass NG_TO_G<string Str, Intrinsic Intrin> {
1898 [(set Int32Regs:$result, (Intrin Int32Regs:$src))]>;
1901 [(set Int64Regs:$result, (Intrin Int64Regs:$src))]>;
1906 [(set Int64Regs:$result, (Intrin Int32Regs:$src))]>,
1910 multiclass G_TO_NG<string Str, Intrinsic Intrin> {
1913 [(set Int32Regs:$result, (Intrin Int32Regs:$src))]>;
1916 [(set Int64Regs:$result, (Intrin Int64Regs:$src))]>;
1921 [(set Int32Regs:$result, (Intrin Int64Regs:$src))]>,
DNVPTXISelLowering.cpp4913 SDValue Intrin = N->getOperand(1); in ReplaceINTRINSIC_W_CHAIN() local
4917 unsigned IntrinNo = cast<ConstantSDNode>(Intrin.getNode())->getZExtValue(); in ReplaceINTRINSIC_W_CHAIN()

12