[Bug] Cannot find intrinsic declaration, possible type mismatch: llvm.sqrt #17952
Description
Actual behavior
Traceback (most recent call last):
File "/data/qshenaf/remote_pc/TirFuzz/bugs/05-11_03-53/topi.rsqrt_4.py", line 9, in <module>
tvm.build(sch.mod, target='llvm')
File "/data/qshenaf/envs/tvm/python/tvm/driver/build_module.py", line 59, in build
return tvm.tir.build(mod, target, pipeline)
^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/python/tvm/tir/build.py", line 186, in build
return tir_to_runtime(host_mod, device_mod_dict, target_host)
^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/python/tvm/tir/build.py", line 98, in tir_to_runtime
mhost = codegen_build(mhost_all, target_host)
^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/python/tvm/tir/build.py", line 80, in codegen_build
return bf(mod, target)
^^^^^^^^^^^^^^^
File "tvm/_ffi/_cython/./packed_func.pxi", line 339, in tvm._ffi._cy3.core.PackedFuncBase.__call__
File "tvm/_ffi/_cython/./packed_func.pxi", line 270, in tvm._ffi._cy3.core.FuncCall
File "tvm/_ffi/_cython/./packed_func.pxi", line 259, in tvm._ffi._cy3.core.FuncCall3
File "tvm/_ffi/_cython/./base.pxi", line 185, in tvm._ffi._cy3.core.CHECK_CALL
File "/data/qshenaf/envs/tvm/python/tvm/_ffi/base.py", line 468, in raise_last_ffi_error
raise py_err
File "/data/qshenaf/envs/tvm/src/target/llvm/llvm_module.cc", line 620, in operator()
n->Init(mod, target);
^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/llvm_module.cc", line 354, in tvm::codegen::LLVMModuleNode::Init(tvm::IRModule const&, tvm::Target const&)
cg->AddFunctionsOrdered(mod->functions.begin(), mod->functions.end());
^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.h", line 180, in void tvm::codegen::CodeGenLLVM::AddFunctionsOrdered<tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator>(tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator)
this->AddFunctionsOrdered(begin, end, [](auto f) { return f; });
^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.h", line 644, in void tvm::codegen::CodeGenLLVM::AddFunctionsOrdered<tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::codegen::CodeGenLLVM::AddFunctionsOrdered<tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator>(tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator)::{lambda(auto:1)#1}>(tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::codegen::CodeGenLLVM::AddFunctionsOrdered<tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator>(tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator)::{lambda(auto:1)#1})
AddFunction(gvar, func);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 232, in tvm::codegen::CodeGenCPU::AddFunction(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
CodeGenLLVM::AddFunction(gvar, func);
^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 223, in tvm::codegen::CodeGenLLVM::AddFunction(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
this->AddFunctionInternal(gvar, f);
^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 312, in tvm::codegen::CodeGenLLVM::AddFunctionInternal(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
this->VisitStmt(f->body);
^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2174, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
VisitStmt(op->body);
^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2174, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
VisitStmt(op->body);
^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2174, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
VisitStmt(op->body);
^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1131, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2118, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AttrStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2174, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
VisitStmt(op->body);
^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2174, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
VisitStmt(op->body);
^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2162, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1131, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2118, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AttrStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2168, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
this->VisitStmt(stmt);
^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2168, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
this->VisitStmt(stmt);
^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1089, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2125, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2174, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
VisitStmt(op->body);
^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2174, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
VisitStmt(op->body);
^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 2168, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
this->VisitStmt(stmt);
^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1099, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
this->CreateComputeScope(op);
^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 578, in tvm::codegen::CodeGenCPU::CreateComputeScope(tvm::tir::AttrStmtNode const*)
this->VisitStmt(op->body);
^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1139, in tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::ForNode const*)
CodeGenLLVM::VisitStmt_(op);
^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 1989, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::ForNode const*)
CreateSerialFor(MakeValue(op->min), MakeValue(op->extent),
^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 873, in tvm::codegen::CodeGenLLVM::CreateSerialFor(llvm::Value*, llvm::Value*, llvm::Value*, tvm::tir::Var const&, tvm::tir::Stmt const&)
this->VisitStmt(body);
^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 1942, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::BufferStoreNode const*)
llvm::Value* value = MakeValue(op->value);
^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.h", line 192, in tvm::codegen::CodeGenLLVM::MakeValue(tvm::PrimExpr const&)
llvm::Value* MakeValue(const PrimExpr& e) { return VisitExpr(e); }
^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 1595, in tvm::codegen::CodeGenLLVM::VisitExpr_(tvm::tir::DivNode const*)
llvm::Value* b = MakeValue(op->b);
^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.h", line 192, in tvm::codegen::CodeGenLLVM::MakeValue(tvm::PrimExpr const&)
llvm::Value* MakeValue(const PrimExpr& e) { return VisitExpr(e); }
^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 1857, in tvm::codegen::CodeGenLLVM::VisitExpr_(tvm::tir::CallNodeconst*)
auto x = CreateIntrinsic(op);
^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc", line 1059, in tvm::codegen::CodeGenCPU::CreateIntrinsic(tvm::tir::CallNode const*)
return CodeGenLLVM::CreateIntrinsic(op);
^^^^^^^^^^^^^^^^^^^^^^^^^^^
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 1361, in tvm::codegen::CodeGenLLVM::CreateIntrinsic(tvm::tir::CallNode const*)
ICHECK(f) << "Cannot find intrinsic declaration, possible type mismatch: "
^^^^^^^^^^^^^^^^^^^^^^^^^^^
tvm.error.InternalError: Traceback (most recent call last):
83: operator()
at /data/qshenaf/envs/tvm/src/target/llvm/llvm_module.cc:620
82: tvm::codegen::LLVMModuleNode::Init(tvm::IRModule const&, tvm::Target const&)
at /data/qshenaf/envs/tvm/src/target/llvm/llvm_module.cc:354
81: void tvm::codegen::CodeGenLLVM::AddFunctionsOrdered<tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator>(tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.h:180
80: void tvm::codegen::CodeGenLLVM::AddFunctionsOrdered<tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::codegen::CodeGenLLVM::AddFunctionsOrdered<tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator>(tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator)::{lambda(auto:1)#1}>(tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::codegen::CodeGenLLVM::AddFunctionsOrdered<tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator>(tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator, tvm::runtime::Map<tvm::GlobalVar, tvm::BaseFunc, void, void>::iterator)::{lambda(auto:1)#1})
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.h:644
79: tvm::codegen::CodeGenCPU::AddFunction(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:232
78: tvm::codegen::CodeGenLLVM::AddFunction(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:223
77: tvm::codegen::CodeGenLLVM::AddFunctionInternal(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:312
76: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
75: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
74: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
73: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
72: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
71: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
70: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
69: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
68: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
67: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
66: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
65: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
64: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
63: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
62: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
61: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
60: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
59: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
58: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
57: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
56: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
55: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
54: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
53: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
52: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
51: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1131
50: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AttrStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2118
49: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
48: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
47: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
46: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
45: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
44: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
43: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
42: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
41: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
40: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1131
39: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AttrStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2118
38: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
37: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
36: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
35: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
34: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2168
33: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
32: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
31: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
30: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
29: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
28: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
27: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
26: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
25: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
24: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
23: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2168
22: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
21: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
20: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
19: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
18: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
17: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
16: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
15: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
14: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
13: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
12: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2168
11: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1099
10: tvm::codegen::CodeGenCPU::CreateComputeScope(tvm::tir::AttrStmtNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:578
9: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::ForNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1139
8: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::ForNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:1989
7: tvm::codegen::CodeGenLLVM::CreateSerialFor(llvm::Value*, llvm::Value*, llvm::Value*, tvm::tir::Var const&, tvm::tir::Stmt const&)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:873
6: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::BufferStoreNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:1942
5: tvm::codegen::CodeGenLLVM::MakeValue(tvm::PrimExpr const&)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.h:192
4: tvm::codegen::CodeGenLLVM::VisitExpr_(tvm::tir::DivNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:1595
3: tvm::codegen::CodeGenLLVM::MakeValue(tvm::PrimExpr const&)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.h:192
2: tvm::codegen::CodeGenLLVM::VisitExpr_(tvm::tir::CallNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:1857
1: tvm::codegen::CodeGenCPU::CreateIntrinsic(tvm::tir::CallNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1059
0: tvm::codegen::CodeGenLLVM::CreateIntrinsic(tvm::tir::CallNode const*)
at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:1361
File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 1361
InternalError: Check failed: (f) is false: Cannot find intrinsic declaration, possible type mismatch: llvm.sqrt
Environment
tvm-0.21.dev0
Steps to reproduce
import tvm
from tvm import te, topi, tir
x = te.placeholder((1024,), dtype='int16', name='x')
op_output = topi.rsqrt(x)
sch = tir.Schedule(te.create_prim_func([x, op_output]))
tvm.build(sch.mod, target='llvm')
Triage
- needs-triage
- topi
cc @jikechao