jikechao opened a new issue, #16286:
URL: https://github.com/apache/tvm/issues/16286
### Actual behavior
```
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:49:5:
error: ‘cudaGraphExec_t’ does not name a type
cudaGraphExec_t exec = nullptr;
^~~~~~~~~~~~~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:
In destructor
‘tvm::runtime::relax_vm::CUDAGraphCache::CaptureResult::~CaptureResult()’:
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:39:11:
error: ‘exec’ was not declared in this scope
if (exec) {
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:39:11:
note: suggested alternative: ‘exit’
if (exec) {
^~~~
exit
In file included from
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:29:0:
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:40:19:
error: ‘cudaGraphExecDestroy’ was not declared in this scope
CUDA_CALL(cudaGraphExecDestroy(exec));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:40:19:
note: suggested alternative: ‘cudaEventDestroy’
CUDA_CALL(cudaGraphExecDestroy(exec));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
[ 22%] Building CXX object
CMakeFiles/tvm_objs.dir/src/meta_schedule/schedule_rule/schedule_rule.cc.o
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:
In member function ‘tvm::runtime::ObjectRef
tvm::runtime::relax_vm::CUDAGraphCache::RunOrCapture(tvm::runtime::relax_vm::VirtualMachine*,
const tvm::runtime::ObjectRef&, tvm::runtime::ObjectRef, int64_t)’:
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:68:19:
error: 2 names provided for structured binding
const auto& [states, exec] = it->second;
^~~~~~~~~~~~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:68:19:
note: while ‘const tvm::runtime::relax_vm::CUDAGraphCache::CaptureResult’
decomposes into 1 element
In file included from
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:29:0:
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:69:17:
error: ‘cudaGraphLaunch’ was not declared in this scope
CUDA_CALL(cudaGraphLaunch(exec,
CUDAThreadEntry::ThreadLocal()->stream));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:69:17:
note: suggested alternative: ‘cudaLaunch’
CUDA_CALL(cudaGraphLaunch(exec,
CUDAThreadEntry::ThreadLocal()->stream));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:95:5:
error: ‘cudaGraph_t’ was not declared in this scope
cudaGraph_t graph;
^~~~~~~~~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:95:5:
note: suggested alternative: ‘cudaError_t’
cudaGraph_t graph;
^~~~~~~~~~~
cudaError_t
In file included from
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:29:0:
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:98:38:
error: ‘cudaStreamCaptureModeGlobal’ was not declared in this scope
cudaStreamCaptureModeGlobal));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:98:38:
note: suggested alternative: ‘cudaStreamCreate’
cudaStreamCaptureModeGlobal));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:97:15:
error: ‘cudaStreamBeginCapture’ was not declared in this scope
CUDA_CALL(cudaStreamBeginCapture(CUDAThreadEntry::ThreadLocal()->stream,
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:97:15:
note: suggested alternative: ‘cudaStreamCreate’
CUDA_CALL(cudaStreamBeginCapture(CUDAThreadEntry::ThreadLocal()->stream,
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:103:77:
error: ‘graph’ was not declared in this scope
CUDA_CALL(cudaStreamEndCapture(CUDAThreadEntry::ThreadLocal()->stream,
&graph));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:103:77:
note: suggested alternative: ‘isgraph’
CUDA_CALL(cudaStreamEndCapture(CUDAThreadEntry::ThreadLocal()->stream,
&graph));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:103:15:
error: ‘cudaStreamEndCapture’ was not declared in this scope
CUDA_CALL(cudaStreamEndCapture(CUDAThreadEntry::ThreadLocal()->stream,
&graph));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:103:15:
note: suggested alternative: ‘cudaStreamCreate’
CUDA_CALL(cudaStreamEndCapture(CUDAThreadEntry::ThreadLocal()->stream,
&graph));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:107:65:
error: ‘std::unordered_map<long int,
tvm::runtime::relax_vm::CUDAGraphCache::CaptureResult>::mapped_type {aka struct
tvm::runtime::relax_vm::CUDAGraphCache::CaptureResult}’ has no member named
‘exec’
CUDA_CALL(cudaGraphInstantiate(&capture_cache_[entry_index].exec,
graph, NULL, NULL, 0));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:107:71:
error: ‘graph’ was not declared in this scope
CUDA_CALL(cudaGraphInstantiate(&capture_cache_[entry_index].exec,
graph, NULL, NULL, 0));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:107:71:
note: suggested alternative: ‘isgraph’
CUDA_CALL(cudaGraphInstantiate(&capture_cache_[entry_index].exec,
graph, NULL, NULL, 0));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:107:15:
error: ‘cudaGraphInstantiate’ was not declared in this scope
CUDA_CALL(cudaGraphInstantiate(&capture_cache_[entry_index].exec,
graph, NULL, NULL, 0));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:107:15:
note: suggested alternative: ‘cudaGraphicsCubeFace’
CUDA_CALL(cudaGraphInstantiate(&capture_cache_[entry_index].exec,
graph, NULL, NULL, 0));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:109:32:
error: ‘graph’ was not declared in this scope
CUDA_CALL(cudaGraphDestroy(graph));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:109:32:
note: suggested alternative: ‘isgraph’
CUDA_CALL(cudaGraphDestroy(graph));
^
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/../../cuda/cuda_common.h:49:22:
note: in definition of macro ‘CUDA_CALL’
cudaError_t e = (func); \
^~~~
/home/shenqingchao/software/tvm-relax/src/runtime/relax_vm/cuda/cuda_graph_builtin.cc:109:15:
error: ‘cudaGraphDestroy’ was not declared in this scope
CUDA_CALL(cudaGraphDestroy(graph));
^
```
### Environment
Ubuntu 18.04
llvm: 2.0
gcc: 3.26
tvm: latest in unity branch
--
This is an automated message from the Apache Git Service.
To respond to the message, please log on to GitHub and use the
URL above to go to the specific comment.
To unsubscribe, e-mail: [email protected]
For queries about this service, please contact Infrastructure at:
[email protected]
