| /external/llvm-project/mlir/lib/Target/LLVMIR/ |
| D | ConvertToNVVMIR.cpp | 71 auto llvmModule = LLVM::ModuleTranslation::translateModule<ModuleTranslation>( in translateModuleToNVVMIR() local
73 if (!llvmModule) in translateModuleToNVVMIR()
74 return llvmModule; in translateModuleToNVVMIR()
83 auto *llvmFunc = llvmModule->getFunction(func.getName()); in translateModuleToNVVMIR()
87 llvm::MDString::get(llvmModule->getContext(), "kernel"), in translateModuleToNVVMIR()
89 llvm::Type::getInt32Ty(llvmModule->getContext()), 1))}; in translateModuleToNVVMIR()
91 llvm::MDNode::get(llvmModule->getContext(), llvmMetadata); in translateModuleToNVVMIR()
92 llvmModule->getOrInsertNamedMetadata("nvvm.annotations") in translateModuleToNVVMIR()
96 return llvmModule; in translateModuleToNVVMIR()
105 auto llvmModule = mlir::translateModuleToNVVMIR(module, llvmContext); in registerToNVVMIRTranslation() local
[all …]
|
| D | ConvertToLLVMIR.cpp | 29 auto llvmModule = in translateModuleToLLVMIR() local
31 if (!llvmModule) in translateModuleToLLVMIR()
33 else if (verifyModule(*llvmModule)) in translateModuleToLLVMIR()
35 return llvmModule; in translateModuleToLLVMIR()
44 auto llvmModule = LLVM::ModuleTranslation::translateModule<>( in registerToLLVMIRTranslation() local
46 if (!llvmModule) in registerToLLVMIRTranslation()
49 llvmModule->print(output, nullptr); in registerToLLVMIRTranslation()
|
| D | ConvertToROCDLIR.cpp | 81 auto llvmModule = LLVM::ModuleTranslation::translateModule<ModuleTranslation>( in translateModuleToROCDLIR() local
93 auto *llvmFunc = llvmModule->getFunction(func.getName()); in translateModuleToROCDLIR()
100 return llvmModule; in translateModuleToROCDLIR()
109 auto llvmModule = mlir::translateModuleToROCDLIR(module, llvmContext); in registerToROCDLIRTranslation() local
110 if (!llvmModule) in registerToROCDLIRTranslation()
113 llvmModule->print(output, nullptr); in registerToROCDLIRTranslation()
|
| D | DebugTranslation.cpp | 27 DebugTranslation::DebugTranslation(Operation *module, llvm::Module &llvmModule) in DebugTranslation() argument
28 : builder(llvmModule), llvmCtx(llvmModule.getContext()), in DebugTranslation()
43 builder.createFile(llvmModule.getModuleIdentifier(), "/"), in DebugTranslation()
48 if (!llvmModule.getModuleFlag(debugVersionKey)) in DebugTranslation()
49 llvmModule.addModuleFlag(llvm::Module::Warning, debugVersionKey, in DebugTranslation()
59 llvmModule.addModuleFlag(llvm::Module::Warning, "CodeView", 1); in DebugTranslation()
|
| D | LLVMAVX512Intr.cpp | 51 auto llvmModule = translateLLVMAVX512ModuleToLLVMIR( in registerAVX512ToLLVMIRTranslation() local
53 if (!llvmModule) in registerAVX512ToLLVMIRTranslation()
56 llvmModule->print(output, nullptr); in registerAVX512ToLLVMIRTranslation()
|
| D | ModuleTranslation.cpp | 179 llvmModule->getContext(), ArrayRef<char>{stringAttr.getValue().data(), in getLLVMConstant()
304 std::unique_ptr<llvm::Module> llvmModule) in ModuleTranslation() argument
305 : mlirModule(module), llvmModule(std::move(llvmModule)), in ModuleTranslation()
307 std::make_unique<DebugTranslation>(module, *this->llvmModule)), in ModuleTranslation()
309 typeTranslator(this->llvmModule->getContext()) { in ModuleTranslation()
394 llvm::LLVMContext &llvmContext = llvmModule->getContext(); in convertOmpParallel()
491 llvm::LLVMContext &llvmContext = llvmModule->getContext(); in convertOmpMaster()
523 ompBuilder = std::make_unique<llvm::OpenMPIRBuilder>(*llvmModule); in convertOmpOperation()
698 llvm::MDBuilder(llvmModule->getContext()) in convertOperation()
784 llvmModule->getContext(), strAttr.getValue(), /*AddNull=*/false); in convertGlobals()
[all …]
|
| D | DebugTranslation.h | 31 DebugTranslation(Operation *module, llvm::Module &llvmModule);
|
| D | ConvertFromLLVMIR.cpp | 838 mlir::translateLLVMIRToModule(std::unique_ptr<llvm::Module> llvmModule, in translateLLVMIRToModule() argument
845 for (llvm::GlobalVariable &gv : llvmModule->globals()) { in translateLLVMIRToModule()
849 for (llvm::Function &f : llvmModule->functions()) { in translateLLVMIRToModule()
863 std::unique_ptr<llvm::Module> llvmModule = llvm::parseIR( in translateLLVMIRToModule() local
865 if (!llvmModule) { in translateLLVMIRToModule()
872 return translateLLVMIRToModule(std::move(llvmModule), context); in translateLLVMIRToModule()
|
| /external/llvm-project/mlir/lib/Conversion/GPUCommon/ |
| D | ConvertKernelFuncToBlob.cpp | 64 std::unique_ptr<llvm::Module> llvmModule = in runOnOperation() local
66 if (!llvmModule) in runOnOperation()
72 *llvmModule, module.getLoc(), module.getName())) in runOnOperation()
85 OwnedBlob convertModuleToBlob(llvm::Module &llvmModule, Location loc,
90 StringAttr translateGPUModuleToBinaryAnnotation(llvm::Module &llvmModule,
119 OwnedBlob GpuKernelToBlobPass::convertModuleToBlob(llvm::Module &llvmModule, in convertModuleToBlob() argument
139 llvmModule.setDataLayout(targetMachine->createDataLayout()); in convertModuleToBlob()
141 auto targetISA = translateModuleToISA(llvmModule, *targetMachine); in convertModuleToBlob()
147 llvm::Module &llvmModule, Location loc, StringRef name) { in translateGPUModuleToBinaryAnnotation() argument
148 auto blob = convertModuleToBlob(llvmModule, loc, name); in translateGPUModuleToBinaryAnnotation()
|
| /external/tensorflow/tensorflow/compiler/mlir/tools/kernel_gen/transforms/ |
| D | gpu_kernel_to_blob_pass.cc | 93 auto llvmModule = mlir::translateModuleToLLVMIR(gpu_module, llvmContext); in GetGpuBinaryBlob() local
96 if (!llvmModule) { in GetGpuBinaryBlob()
100 llvmModule->setModuleIdentifier("acme"); in GetGpuBinaryBlob()
122 auto llvm_module_copy = llvm::CloneModule(*llvmModule); in GetGpuBinaryBlob()
146 if (!llvmModule) { in GetGpuBinaryBlob()
150 llvmModule->setModuleIdentifier("acme"); in GetGpuBinaryBlob()
151 llvmModule->setDataLayout(xla::gpu::nvptx::kDataLayout); in GetGpuBinaryBlob()
187 auto llvm_module_copy = llvm::CloneModule(*llvmModule); in GetGpuBinaryBlob()
|
| /external/llvm-project/mlir/include/mlir/Target/LLVMIR/ |
| D | ModuleTranslation.h | 60 std::unique_ptr<llvm::Module> llvmModule = variable
65 T translator(m, std::move(llvmModule));
73 return std::move(translator.llvmModule);
85 std::unique_ptr<llvm::Module> llvmModule);
128 std::unique_ptr<llvm::Module> llvmModule; variable
|
| /external/llvm-project/mlir/lib/ExecutionEngine/ |
| D | ExecutionEngine.cpp | 113 bool ExecutionEngine::setupTargetTriple(Module *llvmModule) { in setupTargetTriple() argument
137 llvmModule->setDataLayout(machine->createDataLayout()); in setupTargetTriple()
138 llvmModule->setTargetTriple(targetTriple); in setupTargetTriple()
233 auto llvmModule = llvmModuleBuilder ? llvmModuleBuilder(m, *ctx) in create() local
235 if (!llvmModule) in create()
240 setupTargetTriple(llvmModule.get()); in create()
241 packFunctionArguments(llvmModule.get()); in create()
243 auto dataLayout = llvmModule->getDataLayout(); in create()
302 ThreadSafeModule tsm(std::move(llvmModule), std::move(ctx)); in create()
|
| /external/llvm-project/mlir/examples/toy/Ch6/ |
| D | toyc.cpp | 194 auto llvmModule = mlir::translateModuleToLLVMIR(module, llvmContext); in dumpLLVMIR() local
195 if (!llvmModule) { in dumpLLVMIR()
203 mlir::ExecutionEngine::setupTargetTriple(llvmModule.get()); in dumpLLVMIR()
209 if (auto err = optPipeline(llvmModule.get())) { in dumpLLVMIR()
213 llvm::errs() << *llvmModule << "\n"; in dumpLLVMIR()
|
| /external/llvm-project/mlir/examples/toy/Ch7/ |
| D | toyc.cpp | 195 auto llvmModule = mlir::translateModuleToLLVMIR(module, llvmContext); in dumpLLVMIR() local
196 if (!llvmModule) { in dumpLLVMIR()
204 mlir::ExecutionEngine::setupTargetTriple(llvmModule.get()); in dumpLLVMIR()
210 if (auto err = optPipeline(llvmModule.get())) { in dumpLLVMIR()
214 llvm::errs() << *llvmModule << "\n"; in dumpLLVMIR()
|
| /external/llvm-project/mlir/docs/Tutorials/Toy/ |
| D | Ch-6.md | 184 std::unique_ptr<llvm::Module> llvmModule = mlir::translateModuleToLLVMIR(module);
185 if (!llvmModule)
251 auto llvmModule = mlir::translateModuleToLLVMIR(module, llvmContext);
252 if (!llvmModule) {
260 mlir::ExecutionEngine::setupTargetTriple(llvmModule.get());
266 if (auto err = optPipeline(llvmModule.get())) {
270 llvm::errs() << *llvmModule << "\n";
|
| /external/llvm-project/mlir/include/mlir/Target/ |
| D | LLVMIR.h | 45 translateLLVMIRToModule(std::unique_ptr<llvm::Module> llvmModule,
|
| /external/llvm-project/mlir/include/mlir/ExecutionEngine/ |
| D | ExecutionEngine.h | 110 static bool setupTargetTriple(llvm::Module *llvmModule);
|
| /external/llvm-project/mlir/tools/mlir-rocm-runner/ |
| D | mlir-rocm-runner.cpp | 206 auto llvmModule = translateModuleToROCDLIR(m, llvmContext, name); in compileModuleToROCDLIR() local
209 return llvmModule; in compileModuleToROCDLIR()
|