Update more crates to edition 2024.

Three kinds of changes are required.
- Unsafe operations within unsafe functions now need to be explicitly
  marked with `unsafe`.
  - This requires setting `.wrap_unsafe_ops` for unsafe functions
    generated by bindgen.
- `extern "C"` blocks now need to be marked as unsafe.
- `cargo fmt` formats some things slightly different in edition 2024.

Author: nnethercote

crates/blastoff/Cargo.toml

@@ -1,7 +1,7 @@
 [package]
 name = "blastoff"
 version = "0.1.0"
-edition = "2021"
+edition = "2024"
 authors = ["Riccardo D'Ambrosio <[email protected]>"]
 repository = "https://github.com/Rust-GPU/rust-cuda"
 

crates/blastoff/src/context.rs

@@ -320,9 +320,11 @@ impl CublasContext {
     ///
     /// The callback must not panic and unwind.
     pub unsafe fn set_logger_callback(callback: Option<unsafe extern "C" fn(*const c_char)>) {
-        cublas_sys::cublasSetLoggerCallback(callback)
-            .to_result()
-            .unwrap();
+        unsafe {
+            cublas_sys::cublasSetLoggerCallback(callback)
+                .to_result()
+                .unwrap();
+        }
     }
 
     /// Gets the logger callback that was previously set.

crates/blastoff/src/error.rs

@@ -38,8 +38,8 @@ pub trait ToResult {
 
 impl ToResult for cublas_sys::cublasStatus_t {
     fn to_result(self) -> Result<(), CublasError> {
-        use cust_raw::cublas_sys::cublasStatus_t::*;
         use CublasError::*;
+        use cust_raw::cublas_sys::cublasStatus_t::*;
 
         Err(match self {
             CUBLAS_STATUS_SUCCESS => return Ok(()),
@@ -58,8 +58,8 @@ impl ToResult for cublas_sys::cublasStatus_t {
 
 impl CublasError {
     pub fn into_raw(self) -> cublas_sys::cublasStatus_t {
-        use cust_raw::cublas_sys::cublasStatus_t::*;
         use CublasError::*;
+        use cust_raw::cublas_sys::cublasStatus_t::*;
 
         match self {
             NotInitialized => CUBLAS_STATUS_NOT_INITIALIZED,

crates/blastoff/src/level1.rs

@@ -1,10 +1,10 @@
 //! Scalar and Vector-based operations
 
 use crate::{
+    BlasDatatype, Float,
     context::CublasContext,
     error::{Error, ToResult},
     raw::{ComplexLevel1, FloatLevel1, Level1},
-    BlasDatatype, Float,
 };
 use cust::memory::{GpuBox, GpuBuffer};
 use cust::stream::Stream;

crates/blastoff/src/level3.rs

@@ -1,8 +1,8 @@
 use crate::{
+    GemmDatatype, MatrixOp,
     context::CublasContext,
     error::{Error, ToResult},
     raw::GemmOps,
-    GemmDatatype, MatrixOp,
 };
 use cust::memory::{GpuBox, GpuBuffer};
 use cust::stream::Stream;