Skip to content

[Bug] TVMError: unknown intrinsic Op(tir.acos) #17944

New issue
New issue
Closed
#17945
Closed
[Bug] TVMError: unknown intrinsic Op(tir.acos)#17944
#17945
Labels
needs-triagePRs or issues that need to be investigated by maintainers to find the right assignees to address ittype: bug
@jikechao

Description

@jikechao
jikechao
opened on May 10, 2025

Actual behavior

Traceback (most recent call last):
  File "/data/qshenaf/remote_pc/TirFuzz/bugs/05-10_00-36/topi.acos_1.py", line 11, 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_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_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_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 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 1942, in tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::BufferStoreNodeconst*)
    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 1857, in tvm::codegen::CodeGenLLVM::VisitExpr_(tvm::tir::CallNode const*)
    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 1512, in tvm::codegen::CodeGenLLVM::CreateIntrinsic(tvm::tir::CallNode const*)
    LOG(FATAL) << "unknown intrinsic " << op->op;
                  ^^^^^^^^^^^^^^^^^^^^^^^^^^^
tvm._ffi.base.TVMError: Traceback (most recent call last):
  89: operator()
        at /data/qshenaf/envs/tvm/src/target/llvm/llvm_module.cc:620
  88: tvm::codegen::LLVMModuleNode::Init(tvm::IRModule const&, tvm::Target const&)
        at /data/qshenaf/envs/tvm/src/target/llvm/llvm_module.cc:354
  87: 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
  86: 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
  85: tvm::codegen::CodeGenCPU::AddFunction(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:232
  84: tvm::codegen::CodeGenLLVM::AddFunction(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:223
  83: tvm::codegen::CodeGenLLVM::AddFunctionInternal(tvm::GlobalVar const&, tvm::tir::PrimFunc const&)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:312
  82: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  81: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  80: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  79: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  78: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  77: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  76: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
  75: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  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::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  71: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  70: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  69: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  68: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  67: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  66: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  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::DeclBufferNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
  61: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  60: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
  59: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  58: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  57: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1131
  56: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AttrStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2118
  55: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  54: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  53: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  52: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  51: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  50: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
  49: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  48: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
  47: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  46: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1131
  45: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AttrStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2118
  44: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  43: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  42: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  41: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  40: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  39: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  38: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2168
  37: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  36: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  35: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  34: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  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::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2168
  24: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1089
  23: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::AssertStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2125
  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::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
  15: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::DeclBufferNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2174
  14: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::SeqStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2168
  13: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::AttrStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1099
  12: tvm::codegen::CodeGenCPU::CreateComputeScope(tvm::tir::AttrStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:578
  11: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::ForNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1139
  10: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::ForNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:1989
  9: 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
  8: tvm::codegen::CodeGenCPU::VisitStmt_(tvm::tir::ForNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_cpu.cc:1139
  7: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::ForNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:1989
  6: 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
  5: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::LetStmtNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:2162
  4: tvm::codegen::CodeGenLLVM::VisitStmt_(tvm::tir::BufferStoreNode const*)
        at /data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc:1942
  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:1512
  File "/data/qshenaf/envs/tvm/src/target/llvm/codegen_llvm.cc", line 1512
TVMError: unknown intrinsic Op(tir.acos)

Environment

tvm-0.21.dev0

Steps to reproduce

import tvm
from tvm import te, topi, tir


x = te.placeholder([4, 4], dtype='int16', name='x')
op_output = topi.acos(x)

sch = tir.Schedule(te.create_prim_func([x, op_output]))

with tvm.transform.PassContext(opt_level=1):
    tvm.build(sch.mod, target='llvm')

Triage

  • needs-triage
  • topi

Metadata

Metadata

Assignees

No one assigned

    Labels

    needs-triagePRs or issues that need to be investigated by maintainers to find the right assignees to address ittype: bug

    Type

    No type

    Projects

    No projects

    Milestone

    No milestone

    Relationships

    None yet

    Development

    No branches or pull requests

    Issue actions