You are viewing a plain text version of this content. The canonical link for it is here.
Posted to commits@tvm.apache.org by "jikechao (via GitHub)" <gi...@apache.org> on 2023/12/28 07:38:38 UTC

[I] [Bug][Relax] build tvm from source failed relax_vm/cuda/cuda_graph_builtin.cc [tvm]

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: commits-unsubscribe@tvm.apache.org.apache.org

For queries about this service, please contact Infrastructure at:
users@infra.apache.org


Re: [I] [Bug][Relax] build tvm from source failed relax_vm/cuda/cuda_graph_builtin.cc [tvm]

Posted by "junrushao (via GitHub)" <gi...@apache.org>.
junrushao commented on issue #16286:
URL: https://github.com/apache/tvm/issues/16286#issuecomment-1870911876

   Cuda 11.4 has been many years old. You may want to upgrade to at least 11.7 or 12.1


-- 
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: commits-unsubscribe@tvm.apache.org

For queries about this service, please contact Infrastructure at:
users@infra.apache.org


Re: [I] [Bug][Relax] build tvm from source failed relax_vm/cuda/cuda_graph_builtin.cc [tvm]

Posted by "tqchen (via GitHub)" <gi...@apache.org>.
tqchen closed issue #16286: [Bug][Relax] build tvm from source failed relax_vm/cuda/cuda_graph_builtin.cc
URL: https://github.com/apache/tvm/issues/16286


-- 
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: commits-unsubscribe@tvm.apache.org

For queries about this service, please contact Infrastructure at:
users@infra.apache.org


Re: [I] [Bug][Relax] build tvm from source failed relax_vm/cuda/cuda_graph_builtin.cc [tvm]

Posted by "jikechao (via GitHub)" <gi...@apache.org>.
jikechao commented on issue #16286:
URL: https://github.com/apache/tvm/issues/16286#issuecomment-1870917077

   @junrushao Thanks! I'll have a try.


-- 
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: commits-unsubscribe@tvm.apache.org

For queries about this service, please contact Infrastructure at:
users@infra.apache.org


Re: [I] [Bug][Relax] build tvm from source failed relax_vm/cuda/cuda_graph_builtin.cc [tvm]

Posted by "jikechao (via GitHub)" <gi...@apache.org>.
jikechao commented on issue #16286:
URL: https://github.com/apache/tvm/issues/16286#issuecomment-1870910784

   BTW, my environment can build TVM in the master branch well but building the source code of tvm in the unity branch failed.


-- 
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: commits-unsubscribe@tvm.apache.org

For queries about this service, please contact Infrastructure at:
users@infra.apache.org