diff --git a/crates/specialized/rtx-cfd/src/solvers/lbm/d2q9_gpu.rs b/crates/specialized/rtx-cfd/src/solvers/lbm/d2q9_gpu.rs index be8f798..64cc309 100644 --- a/crates/specialized/rtx-cfd/src/solvers/lbm/d2q9_gpu.rs +++ b/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 + )) })?; } } diff --git a/crates/specialized/rtx-cfd/src/solvers/lbm/d3q19_gpu.rs b/crates/specialized/rtx-cfd/src/solvers/lbm/d3q19_gpu.rs index 880f800..a202696 100644 --- a/crates/specialized/rtx-cfd/src/solvers/lbm/d3q19_gpu.rs +++ b/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()?; diff --git a/crates/specialized/rtx-cfd/src/turbulence/k_epsilon_gpu.rs b/crates/specialized/rtx-cfd/src/turbulence/k_epsilon_gpu.rs index 3abe407..4096fc1 100644 --- a/crates/specialized/rtx-cfd/src/turbulence/k_epsilon_gpu.rs +++ b/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)) + })?; } } diff --git a/crates/specialized/rtx-cfd/src/turbulence/smagorinsky_gpu.rs b/crates/specialized/rtx-cfd/src/turbulence/smagorinsky_gpu.rs index c47dfb6..cc15ff9 100644 --- a/crates/specialized/rtx-cfd/src/turbulence/smagorinsky_gpu.rs +++ b/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 + )) })?; } } diff --git a/crates/specialized/rtx-cfd/tests/cuda_kernel_manager_tests.rs b/crates/specialized/rtx-cfd/tests/cuda_kernel_manager_tests.rs index 3c15c78..bc5cc4e 100644 --- a/crates/specialized/rtx-cfd/tests/cuda_kernel_manager_tests.rs +++ b/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() } } diff --git a/crates/specialized/rtx-cfd/tests/gpu_kernel_tests.rs b/crates/specialized/rtx-cfd/tests/gpu_kernel_tests.rs index 46876e2..2f7ea38 100644 --- a/crates/specialized/rtx-cfd/tests/gpu_kernel_tests.rs +++ b/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() } } diff --git a/crates/specialized/rtx-cfd/tests/gpu_reduction_tests.rs b/crates/specialized/rtx-cfd/tests/gpu_reduction_tests.rs index c426fba..cd02c08 100644 --- a/crates/specialized/rtx-cfd/tests/gpu_reduction_tests.rs +++ b/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() } } diff --git a/crates/specialized/rtx-cfd/tests/kernels_tests.rs b/crates/specialized/rtx-cfd/tests/kernels_tests.rs index 40d435a..8f536b3 100644 --- a/crates/specialized/rtx-cfd/tests/kernels_tests.rs +++ b/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)?;