Skip to content

cubecl-hip: Build failures when trying to build with ROCM support #922

@hodgesds

Description

@hodgesds

Environment: Arch linux, 6.14 kernel

$ clang -v
clang version 20.1.8
Target: x86_64-pc-linux-gnu
Thread model: posix
InstalledDir: /usr/bin
Found candidate GCC installation: /usr/bin/../lib/gcc/x86_64-pc-linux-gnu/15.2.1
Found candidate GCC installation: /usr/bin/../lib64/gcc/x86_64-pc-linux-gnu/15.2.1
Selected GCC installation: /usr/bin/../lib64/gcc/x86_64-pc-linux-gnu/15.2.1
Candidate multilib: .;@m64
Candidate multilib: 32;@m32
Selected multilib: .;@m64
Found HIP installation: /opt/rocm, version 6.4.43484
$ vulkaninfo | grep driver
'DISPLAY' environment variable not set... skipping surface info
        VK_LUNARG_direct_driver_loading        : extension revision 1
        driverVersion     = 2.0.349 (8388957)
        driverUUID                        = 414d442d-4c49-4e55-582d-445256000000
        driverID                                             = DRIVER_ID_AMD_OPEN_SOURCE
        driverName                                           = AMD open-source driver
        driverInfo                                           = 2025.Q2.1 (LLPC)
        VK_KHR_driver_properties                    : extension revision 1
        driverVersion     = 2.0.349 (8388957)
        driverUUID                        = 414d442d-4c49-4e55-582d-445256000000
        driverID                                             = DRIVER_ID_AMD_OPEN_SOURCE
        driverName                                           = AMD open-source driver
        driverInfo                                           = 2025.Q2.1 (LLPC)
        VK_KHR_driver_properties                    : extension revision 1

Build error:

error[E0432]: unresolved imports `cubecl_hip_sys::HIP_SUCCESS`, `cubecl_hip_sys::hiprtcResult_HIPRTC_SUCCESS`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:15:22
   |
15 | use cubecl_hip_sys::{HIP_SUCCESS, get_hip_include_path, hiprtcResult_HIPRTC_SUCCESS};
   |                      ^^^^^^^^^^^                        ^^^^^^^^^^^^^^^^^^^^^^^^^^^ no `hiprtcResult_HIPRTC_SUCCESS` in the root
   |                      |
   |                      no `HIP_SUCCESS` in the root

error[E0432]: unresolved import `cubecl_hip_sys::HIP_SUCCESS`
 --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:1:5
  |
1 | use cubecl_hip_sys::HIP_SUCCESS;
  |     ^^^^^^^^^^^^^^^^^^^^^^^^^^^ no `HIP_SUCCESS` in the root

error[E0432]: unresolved import `cubecl_hip_sys::HIP_SUCCESS`
 --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:1:5
  |
1 | use cubecl_hip_sys::HIP_SUCCESS;
  |     ^^^^^^^^^^^^^^^^^^^^^^^^^^^ no `HIP_SUCCESS` in the root

error[E0432]: unresolved import `cubecl_hip_sys::HIP_SUCCESS`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/runtime.rs:16:5
   |
16 | use cubecl_hip_sys::HIP_SUCCESS;
   |     ^^^^^^^^^^^^^^^^^^^^^^^^^^^ no `HIP_SUCCESS` in the root

   Compiling clap_builder v4.5.48
error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:42:29
   |
42 |     stream: cubecl_hip_sys::hipStream_t,
   |                             ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipModule_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:61:30
   |
61 |     _module: cubecl_hip_sys::hipModule_t,
   |                              ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipFunction_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:62:27
   |
62 |     func: cubecl_hip_sys::hipFunction_t,
   |                           ^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipMemcpyDtoHAsync` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:78:42
   |
78 |             let status = cubecl_hip_sys::hipMemcpyDtoHAsync(
   |                                          ^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipMemcpyDtoHAsync` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:105:46
    |
105 |                 let status = cubecl_hip_sys::hipMemcpyDtoHAsync(
    |                                              ^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:303:33
    |
303 |         stream: cubecl_hip_sys::hipStream_t,
    |                                 ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipStreamSynchronize` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:326:42
    |
326 |             let status = cubecl_hip_sys::hipStreamSynchronize(self.stream);
    |                                          ^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hiprtcProgram` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:381:46
    |
381 |             let mut program: cubecl_hip_sys::hiprtcProgram = std::ptr::null_mut();
    |                                              ^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hiprtcCreateProgram` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:382:42
    |
382 |             let status = cubecl_hip_sys::hiprtcCreateProgram(
    |                                          ^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hiprtcCompileProgram` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:412:33
    |
412 |                 cubecl_hip_sys::hiprtcCompileProgram(program, options.len() as i32, options_ptr);
    |                                 ^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hiprtcGetProgramLogSize` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:416:37
    |
416 |                     cubecl_hip_sys::hiprtcGetProgramLogSize(program, &mut log_size as *mut usize);
    |                                     ^^^^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hiprtcGetProgramLog` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:422:46
    |
422 |                 let status = cubecl_hip_sys::hiprtcGetProgramLog(program, log_buffer.as_mut_ptr());
    |                                              ^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hiprtcGetCodeSize` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:448:42
    |
448 |             let status = cubecl_hip_sys::hiprtcGetCodeSize(program, &mut code_size);
    |                                          ^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hiprtcGetCode` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:456:42
    |
456 |             let status = cubecl_hip_sys::hiprtcGetCode(program, code.as_mut_ptr());
    |                                          ^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipModule_t` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:497:41
    |
497 |         let mut module: cubecl_hip_sys::hipModule_t = std::ptr::null_mut();
    |                                         ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipModuleLoadData` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:500:42
    |
500 |             let status = cubecl_hip_sys::hipModuleLoadData(&mut module, codeptr as *const _);
    |                                          ^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipFunction_t` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:504:39
    |
504 |         let mut func: cubecl_hip_sys::hipFunction_t = std::ptr::null_mut();
    |                                       ^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipModuleGetFunction` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:507:33
    |
507 |                 cubecl_hip_sys::hipModuleGetFunction(&mut func, module, func_name.as_ptr());
    |                                 ^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipModuleLaunchKernel` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:537:42
    |
537 |             let status = cubecl_hip_sys::hipModuleLaunchKernel(
    |                                          ^^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find value `hipError_t_hipErrorOutOfMemory` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:553:42
    |
553 |             if status == cubecl_hip_sys::hipError_t_hipErrorOutOfMemory {
    |                                          ^^^^^^^^^^^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipMemcpyHtoDAsync` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/server.rs:592:42
    |
592 |             let status = cubecl_hip_sys::hipMemcpyHtoDAsync(
    |                                          ^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipDeviceptr_t` in crate `cubecl_hip_sys`
 --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:8:48
  |
8 |     memory: HashMap<StorageId, cubecl_hip_sys::hipDeviceptr_t>,
  |                                                ^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:10:29
   |
10 |     stream: cubecl_hip_sys::hipStream_t,
   |                             ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipDeviceptr_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:11:62
   |
11 |     activate_slices: HashMap<ActiveResource, cubecl_hip_sys::hipDeviceptr_t>,
   |                                                              ^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:30:62
   |
30 |     pub fn new(mem_alignment: usize, stream: cubecl_hip_sys::hipStream_t) -> Self {
   |                                                              ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipFreeAsync` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:45:37
   |
45 |                     cubecl_hip_sys::hipFreeAsync(ptr, self.stream);
   |                                     ^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipDeviceptr_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:56:36
   |
56 | pub type Binding = cubecl_hip_sys::hipDeviceptr_t;
   |                                    ^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipDeviceptr_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:62:30
   |
62 |     pub ptr: cubecl_hip_sys::hipDeviceptr_t,
   |                              ^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipDeviceptr_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:87:57
   |
87 |             .insert(key.clone(), ptr as cubecl_hip_sys::hipDeviceptr_t);
   |                                                         ^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipDeviceptr_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:94:43
   |
94 |             ptr as *const cubecl_hip_sys::hipDeviceptr_t as *mut std::ffi::c_void,
   |                                           ^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipMallocAsync` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/storage.rs:104:42
    |
104 |             let status = cubecl_hip_sys::hipMallocAsync(&mut dptr, size as usize, self.stream);
    |                                          ^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
 --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:9:29
  |
9 |     stream: cubecl_hip_sys::hipStream_t,
  |                             ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipEvent_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:10:28
   |
10 |     event: cubecl_hip_sys::hipEvent_t,
   |                            ^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:27:40
   |
27 |     pub fn new(stream: cubecl_hip_sys::hipStream_t) -> Self {
   |                                        ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipEvent_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:28:40
   |
28 |         let mut event: cubecl_hip_sys::hipEvent_t = std::ptr::null_mut();
   |                                        ^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipEventCreateWithFlags` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:30:42
   |
30 |             let status = cubecl_hip_sys::hipEventCreateWithFlags(
   |                                          ^^^^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find value `hipEventDefault` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:32:33
   |
32 |                 cubecl_hip_sys::hipEventDefault,
   |                                 ^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipEventRecord` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:35:42
   |
35 |             let status = cubecl_hip_sys::hipEventRecord(event, stream);
   |                                          ^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipStreamWaitEvent` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:53:42
   |
53 |             let status = cubecl_hip_sys::hipStreamWaitEvent(self.stream, self.event, 0);
   |                                          ^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipEventDestroy` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:58:42
   |
58 |             let status = cubecl_hip_sys::hipEventDestroy(self.event);
   |                                          ^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:78:29
   |
78 |     stream: cubecl_hip_sys::hipStream_t,
   |                             ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:87:40
   |
87 |     pub fn new(stream: cubecl_hip_sys::hipStream_t) -> Self {
   |                                        ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipStreamSynchronize` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/compute/fence.rs:97:42
   |
97 |             let status = cubecl_hip_sys::hipStreamSynchronize(self.stream);
   |                                          ^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipGetDevicePropertiesR0600` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/runtime.rs:67:38
   |
67 |         let status = cubecl_hip_sys::hipGetDevicePropertiesR0600(
   |                                      ^^^^^^^^^^^^^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipDevice_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/runtime.rs:69:45
   |
69 |             device.index as cubecl_hip_sys::hipDevice_t,
   |                                             ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipSetDevice` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/runtime.rs:97:38
   |
97 |         let status = cubecl_hip_sys::hipSetDevice(device.index as cubecl_hip_sys::hipDevice_t);
   |                                      ^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipDevice_t` in crate `cubecl_hip_sys`
  --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/runtime.rs:97:83
   |
97 |         let status = cubecl_hip_sys::hipSetDevice(device.index as cubecl_hip_sys::hipDevice_t);
   |                                                                                   ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0412]: cannot find type `hipStream_t` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/runtime.rs:105:41
    |
105 |         let mut stream: cubecl_hip_sys::hipStream_t = std::ptr::null_mut();
    |                                         ^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipStreamCreate` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/runtime.rs:106:45
    |
106 |         let stream_status = cubecl_hip_sys::hipStreamCreate(&mut stream);
    |                                             ^^^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

error[E0425]: cannot find function `hipMemGetInfo` in crate `cubecl_hip_sys`
   --> /home/daniel/.cargo/registry/src/index.crates.io-1949cf8c6b5b557f/cubecl-hip-0.6.0/src/runtime.rs:114:38
    |
114 |         let status = cubecl_hip_sys::hipMemGetInfo(
    |                                      ^^^^^^^^^^^^^ not found in `cubecl_hip_sys`

   Compiling env_logger v0.10.2
Some errors have detailed explanations: E0412, E0425, E0432.
For more information about an error, try `rustc --explain E0412`.
error: could not compile `cubecl-hip` (lib) due to 54 previous errors

Related crate deps:

[dependencies]
anyhow = "1.0.65"
burn = { version = "0.18.0", features = ["train", "ndarray", "dataset", "record-item-custom-serde"] }
burn-rocm = { version = "0.18.0", optional = true }
burn-wgpu = { version = "0.18.0", optional = true }
burn-ndarray = "0.18.0"
burn-autodiff = "0.18.0"
burn-train = "0.18.0"
serde = { version = "1.0.226", features = ["derive"] }
csv = "1.1"
clap = { version = "4.5.47", features = ["derive"] }
log = "0.4.20"
env_logger = "0.10.0"
humantime = "2.1.0"

[features]
default = ["wgpu"]
wgpu = ["burn/wgpu", "dep:burn-wgpu"]
rocm = ["burn/rocm", "dep:burn-rocm"]

Metadata

Metadata

Assignees

No one assigned

    Labels

    No labels
    No labels

    Type

    No type

    Projects

    No projects

    Milestone

    No milestone

    Relationships

    None yet

    Development

    No branches or pull requests

    Issue actions