From 2fe3cd80a04c92f3feb8e2e8cad0bf70ad53afd3 Mon Sep 17 00:00:00 2001 From: Martin Bauernfeind Date: Thu, 23 Jun 2022 19:36:59 +0200 Subject: [PATCH] :bug: further refactor step fixing --- src/force.cu | 8 ++++---- 1 file changed, 4 insertions(+), 4 deletions(-) diff --git a/src/force.cu b/src/force.cu index f9329f7..12e59be 100644 --- a/src/force.cu +++ b/src/force.cu @@ -153,7 +153,7 @@ void cuda_final_integrate(bool doReneighbour, Parameter *param, Atom *atom, Atom checkCUDAError( "DeviceSync FinalIntegrate", cudaDeviceSynchronize() ); if(doReneighbour) { - checkCUDAError( "FinalIntegrate: velocity memcpy", cudaMemcpy(atom->vx, c_atom.vx, sizeof(MD_FLOAT) * atom->Nlocal * 3, cudaMemcpyDeviceToHost) ); + checkCUDAError( "FinalIntegrate: velocity memcpy", cudaMemcpy(atom->vx, c_atom->vx, sizeof(MD_FLOAT) * atom->Nlocal * 3, cudaMemcpyDeviceToHost) ); } } @@ -171,9 +171,9 @@ void cuda_initial_integrate(bool doReneighbour, Parameter *param, Atom *atom, At checkCUDAError( "DeviceSync InitialIntegrate", cudaDeviceSynchronize() ); if(doReneighbour) { - checkCUDAError( "InitialIntegrate: velocity memcpy", cudaMemcpy(atom->vx, c_atom.vx, sizeof(MD_FLOAT) * atom->Nlocal * 3, cudaMemcpyDeviceToHost) ); + checkCUDAError( "InitialIntegrate: velocity memcpy", cudaMemcpy(atom->vx, c_atom->vx, sizeof(MD_FLOAT) * atom->Nlocal * 3, cudaMemcpyDeviceToHost) ); } - checkCUDAError( "InitialIntegrate: position memcpy", cudaMemcpy(atom->x, c_atom.x, sizeof(MD_FLOAT) * atom->Nlocal * 3, cudaMemcpyDeviceToHost) ); + checkCUDAError( "InitialIntegrate: position memcpy", cudaMemcpy(atom->x, c_atom->x, sizeof(MD_FLOAT) * atom->Nlocal * 3, cudaMemcpyDeviceToHost) ); } double computeForce( @@ -215,7 +215,7 @@ double computeForce( // HINT: Run with cuda-memcheck ./MDBench-NVCC in case of error - // checkCUDAError( "c_atom.fx memset", cudaMemset(c_atom.fx, 0, sizeof(MD_FLOAT) * Nlocal * 3) ); + // checkCUDAError( "c_atom->fx memset", cudaMemset(c_atom->fx, 0, sizeof(MD_FLOAT) * Nlocal * 3) ); cudaProfilerStart();