rtx-cfd: rustfmt over the repaired GPU modules and tests

crates/specialized/rtx-cfd/src/solvers/lbm/d2q9_gpu.rs

@@ -228,7 +228,10 @@ impl D2Q9GpuSolver {
                     .arg(&(ny as i32))
                     .launch(config)
                     .map_err(|e| {
-                        CfdError::gpu_error(&format!("Equilibrium init kernel launch failed: {}", e))
+                        CfdError::gpu_error(&format!(
+                            "Equilibrium init kernel launch failed: {}",
+                            e
+                        ))
                     })?;
             }
         }

crates/specialized/rtx-cfd/src/solvers/lbm/d3q19_gpu.rs

@@ -406,7 +406,9 @@ __global__ void d3q19_bounce_back_boundaries(
                 .arg(&(buffers.ny as i32))
                 .arg(&(buffers.nz as i32))
                 .launch(config)
-                .map_err(|e| CfdError::gpu_error(&format!("Collision kernel launch failed: {}", e)))?;
+                .map_err(|e| {
+                    CfdError::gpu_error(&format!("Collision kernel launch failed: {}", e))
+                })?;
         }
 
         self.kernel_manager.synchronize()?;
@@ -448,7 +450,9 @@ __global__ void d3q19_bounce_back_boundaries(
                 .arg(&(buffers.ny as i32))
                 .arg(&(buffers.nz as i32))
                 .launch(config)
-                .map_err(|e| CfdError::gpu_error(&format!("Streaming kernel launch failed: {}", e)))?;
+                .map_err(|e| {
+                    CfdError::gpu_error(&format!("Streaming kernel launch failed: {}", e))
+                })?;
         }
 
         // Swap buffers: f = f_temp
@@ -592,7 +596,9 @@ __global__ void d3q19_bounce_back_boundaries(
                 .arg(&(buffers.ny as i32))
                 .arg(&(buffers.nz as i32))
                 .launch(config)
-                .map_err(|e| CfdError::gpu_error(&format!("Boundary kernel launch failed: {}", e)))?;
+                .map_err(|e| {
+                    CfdError::gpu_error(&format!("Boundary kernel launch failed: {}", e))
+                })?;
         }
 
         self.kernel_manager.synchronize()?;

crates/specialized/rtx-cfd/src/turbulence/k_epsilon_gpu.rs

@@ -212,7 +212,10 @@ impl KEpsilonGpuModel {
                     .arg(&(buffers.nz as i32))
                     .launch(config)
                     .map_err(|e| {
-                        CfdError::gpu_error(&format!("Velocity gradients kernel launch failed: {}", e))
+                        CfdError::gpu_error(&format!(
+                            "Velocity gradients kernel launch failed: {}",
+                            e
+                        ))
                     })?;
             }
         }
@@ -427,7 +430,9 @@ impl KEpsilonGpuModel {
                     .arg(&(buffers.ny as i32))
                     .arg(&(buffers.nz as i32))
                     .launch(config)
-                    .map_err(|e| CfdError::gpu_error(&format!("Update kernel launch failed: {}", e)))?;
+                    .map_err(|e| {
+                        CfdError::gpu_error(&format!("Update kernel launch failed: {}", e))
+                    })?;
             }
         }
 

crates/specialized/rtx-cfd/src/turbulence/smagorinsky_gpu.rs

@@ -80,7 +80,11 @@ impl SmagorinskyGpuModel {
     /// Load and compile Smagorinsky CUDA kernels
     fn load_smagorinsky_kernels(&mut self) -> CfdResult<()> {
         // In real implementation, would compile or load PTX for Smagorinsky kernels
-        self.smagorinsky_module = Some(self.kernel_manager.get_module("smagorinsky_kernels")?.clone());
+        self.smagorinsky_module = Some(
+            self.kernel_manager
+                .get_module("smagorinsky_kernels")?
+                .clone(),
+        );
         Ok(())
     }
 
@@ -242,7 +246,10 @@ impl SmagorinskyGpuModel {
                     .arg(&(buffers.nz as i32))
                     .launch(config)
                     .map_err(|e| {
-                        CfdError::gpu_error(&format!("Velocity gradients kernel launch failed: {}", e))
+                        CfdError::gpu_error(&format!(
+                            "Velocity gradients kernel launch failed: {}",
+                            e
+                        ))
                     })?;
             }
         }

crates/specialized/rtx-cfd/tests/cuda_kernel_manager_tests.rs

@@ -20,7 +20,7 @@ mod cuda_kernel_manager_tests {
             viscosity: 0.01,
             density: 1.0,
             device_id: 0,
-        ..CfdConfig::default()
+            ..CfdConfig::default()
         }
     }
 

crates/specialized/rtx-cfd/tests/gpu_kernel_tests.rs

@@ -25,7 +25,7 @@ mod cuda_tests {
             viscosity: 0.01,
             density: 1.0,
             device_id: 0,
-        ..CfdConfig::default()
+            ..CfdConfig::default()
         }
     }
 

crates/specialized/rtx-cfd/tests/gpu_reduction_tests.rs

@@ -21,7 +21,7 @@ mod gpu_reduction_tests {
             viscosity: 0.01,
             density: 1.0,
             device_id: 0,
-        ..CfdConfig::default()
+            ..CfdConfig::default()
         }
     }
 

crates/specialized/rtx-cfd/tests/kernels_tests.rs

@@ -46,7 +46,13 @@ mod cuda_tests {
         d_phi = kernel_manager.copy_to_device(&phi)?;
 
         // Run advection kernel
-        advection_kernel.apply(&d_phi, &mut d_phi_new, velocity as f32, dt as f32, dx as f32)?;
+        advection_kernel.apply(
+            &d_phi,
+            &mut d_phi_new,
+            velocity as f32,
+            dt as f32,
+            dx as f32,
+        )?;
 
         // Copy result back
         let mut result = vec![0.0f32; nx];
@@ -101,7 +107,13 @@ mod cuda_tests {
         let mut d_phi_new = kernel_manager.allocate_f32(nx)?;
 
         d_phi = kernel_manager.copy_to_device(&phi)?;
-        advection_kernel.apply(&d_phi, &mut d_phi_new, velocity as f32, dt as f32, dx as f32)?;
+        advection_kernel.apply(
+            &d_phi,
+            &mut d_phi_new,
+            velocity as f32,
+            dt as f32,
+            dx as f32,
+        )?;
 
         let mut result = vec![0.0f32; nx];
         result = kernel_manager.copy_from_device(&d_phi_new)?;