summaryrefslogtreecommitdiffstats
diff options
context:
space:
mode:
authorWillem Jan Palenstijn <Willem.Jan.Palenstijn@cwi.nl>2020-02-05 14:12:38 +0100
committerWillem Jan Palenstijn <Willem.Jan.Palenstijn@cwi.nl>2020-02-05 14:12:38 +0100
commit59b73103187c04ad63d90d65ef67f3a9fe19d00e (patch)
treeac4d7809a86751e655d3a97ce1bbca9d4a843c4b
parent73e6231f1169a7f88ac9fcf078b2765723f5e842 (diff)
downloadastra-59b73103187c04ad63d90d65ef67f3a9fe19d00e.tar.gz
astra-59b73103187c04ad63d90d65ef67f3a9fe19d00e.tar.bz2
astra-59b73103187c04ad63d90d65ef67f3a9fe19d00e.tar.xz
astra-59b73103187c04ad63d90d65ef67f3a9fe19d00e.zip
Fix memory leaks in 3D BP
-rw-r--r--cuda/3d/cone_bp.cu2
-rw-r--r--cuda/3d/par3d_bp.cu4
2 files changed, 6 insertions, 0 deletions
diff --git a/cuda/3d/cone_bp.cu b/cuda/3d/cone_bp.cu
index 7312bbc..df1e19f 100644
--- a/cuda/3d/cone_bp.cu
+++ b/cuda/3d/cone_bp.cu
@@ -303,6 +303,8 @@ bool transferConstants(const SConeProjection* angles, unsigned int iProjAngles,
// TODO: Check for errors
cudaMemcpyToSymbol(gC_C, p, iProjAngles*sizeof(DevConeParams), 0, cudaMemcpyHostToDevice);
+ delete[] p;
+
return true;
}
diff --git a/cuda/3d/par3d_bp.cu b/cuda/3d/par3d_bp.cu
index 602f209..32a2062 100644
--- a/cuda/3d/par3d_bp.cu
+++ b/cuda/3d/par3d_bp.cu
@@ -247,6 +247,10 @@ bool transferConstants(const SPar3DProjection* angles, unsigned int iProjAngles,
cudaMemcpyToSymbol(gC_C, p, iProjAngles*sizeof(DevPar3DParams), 0, cudaMemcpyHostToDevice);
cudaMemcpyToSymbol(gC_scale, s, iProjAngles*sizeof(float), 0, cudaMemcpyHostToDevice);
+
+ delete[] p;
+ delete[] s;
+
return true;
}