create_image_ID retuns errno_t

Author: oguyon

GPU_SVD_computeControlMatrix.c

@@ -387,7 +387,7 @@ errno_t GPU_SVD_computeControlMatrix(
     save_fits(ID_VTmatrix_name, "!matVT.fits");
 
     cublasStatus_t cublasStat = cublasSgemm(cublasH, CUBLAS_OP_T, CUBLAS_OP_T, n, m, n, &alpha, d_VT,
-                           n, d_U, m, &beta, d_M, n);
+                                            n, d_U, m, &beta, d_M, n);
     if(cublasStat != CUBLAS_STATUS_SUCCESS)
     {
         printf("cublasSgemm returned error code %d, line(%d)\n", cudaStat, __LINE__);
@@ -411,13 +411,14 @@ errno_t GPU_SVD_computeControlMatrix(
     }
 
 
-    ID_Cmatrix = create_image_ID(
-                     ID_Cmatrix_name,
-                     data.image[ID_Rmatrix].md[0].naxis,
-                     arraysizetmp,
-                     _DATATYPE_FLOAT,
-                     0,
-                     0, 0);
+    create_image_ID(
+        ID_Cmatrix_name,
+        data.image[ID_Rmatrix].md[0].naxis,
+        arraysizetmp,
+        _DATATYPE_FLOAT,
+        0,
+        0, 0,
+        &ID_Cmatrix);
 
 
     //   cudaStat = cudaMemcpy(data.image[ID_Cmatrix].array.F, d_M, sizeof(float)*m*n, cudaMemcpyDeviceToHost);

GPU_loop_MultMat_setup.c

@@ -235,8 +235,9 @@ errno_t GPU_loop_MultMat_setup(
             sizearraytmp = (uint32_t *) malloc(sizeof(uint32_t) * 2);
             sizearraytmp[0] = gpumatmultconf[index].M;
             sizearraytmp[1] = 1;
-            gpumatmultconf[index].IDout = create_image_ID(IDoutdmmodes_name, 2,
-                                          sizearraytmp, _DATATYPE_FLOAT, 1, 10, 0);
+            create_image_ID(IDoutdmmodes_name, 2,
+                                          sizearraytmp, _DATATYPE_FLOAT, 1, 10, 0,
+                                          &(gpumatmultconf[index].IDout));
             free(sizearraytmp);
         }
         else

MatMatMult_testPseudoInverse.c

@@ -208,8 +208,8 @@ long CUDACOMP_MatMatMult_testPseudoInverse(
 
     arraysizetmp[0] = N;
     arraysizetmp[1] = N;
-    IDmatOut = create_image_ID(IDmatOut_name, 2, arraysizetmp, _DATATYPE_FLOAT, 0,
-                               0, 0);
+     create_image_ID(IDmatOut_name, 2, arraysizetmp, _DATATYPE_FLOAT, 0,
+                               0, 0, &IDmatOut);
 
 
     for(ii = 0; ii < N * N; ii++)

cudacomp_MVMextractModesLoop.c

@@ -751,7 +751,7 @@ errno_t __attribute__((hot)) CUDACOMP_MVMextractModesLoop_RUN()
 
     ID_modeval = image_ID(IDmodes_val_name);
     if(ID_modeval == -1) { // CREATE IT
-        ID_modeval = create_image_ID(IDmodes_val_name, 2, arraytmp, _DATATYPE_FLOAT, 1, 0, 0);
+        create_image_ID(IDmodes_val_name, 2, arraytmp, _DATATYPE_FLOAT, 1, 0, 0, &ID_modeval);
         COREMOD_MEMORY_image_set_createsem(IDmodes_val_name, 10);
         MODEVALCOMPUTE = 1;
     } else { // USE STREAM, DO NOT COMPUTE IT
@@ -885,7 +885,7 @@ errno_t __attribute__((hot)) CUDACOMP_MVMextractModesLoop_RUN()
             }
         }
         if(imOK == 0) {
-            IDtrace = create_image_ID(traceim_name, 2, sizearraytmp, _DATATYPE_FLOAT, 1, 0, 0);
+            create_image_ID(traceim_name, 2, sizearraytmp, _DATATYPE_FLOAT, 1, 0, 0, &IDtrace);
         }
         COREMOD_MEMORY_image_set_createsem(traceim_name, 10);
         free(sizearraytmp);
@@ -923,7 +923,7 @@ errno_t __attribute__((hot)) CUDACOMP_MVMextractModesLoop_RUN()
             }
         }
         if(imOK == 0) {
-            IDprocave = create_image_ID(process_ave_name, 2, sizearraytmp, _DATATYPE_FLOAT, 1, 0, 0);
+            create_image_ID(process_ave_name, 2, sizearraytmp, _DATATYPE_FLOAT, 1, 0, 0, &IDprocave);
         }
         COREMOD_MEMORY_image_set_createsem(process_ave_name, 10);
         free(sizearraytmp);
@@ -955,7 +955,7 @@ errno_t __attribute__((hot)) CUDACOMP_MVMextractModesLoop_RUN()
             }
         }
         if(imOK == 0) {
-            IDprocrms = create_image_ID(process_rms_name, 2, sizearraytmp, _DATATYPE_FLOAT, 1, 0, 0);
+            create_image_ID(process_rms_name, 2, sizearraytmp, _DATATYPE_FLOAT, 1, 0, 0, &IDprocrms);
         }
         COREMOD_MEMORY_image_set_createsem(process_rms_name, 10);
         free(sizearraytmp);

cudacomptest.c

@@ -66,7 +66,7 @@ errno_t cudacomptest_addCLIcmd()
         "<NB actuators [long]> <NB modes [long]> <NB pixels [long]> <NB GPU [long]>",
         "cudacomptest 1000 20 1000 1",
         "int GPUcomp_test(long NBact, long NBmodes, long WFSsize, long GPUcnt)"
-        );
+    );
 
 
     return RETURN_SUCCESS;
@@ -172,18 +172,18 @@ errno_t GPUcomp_test(
     cmsize[0] = WFSsize;
     cmsize[1] = WFSsize;
     cmsize[2] = NBmodes;
-    ID_contrM = create_image_ID("cudatestcm", 3, cmsize, _DATATYPE_FLOAT, 1, 0, 0);
+    create_image_ID("cudatestcm", 3, cmsize, _DATATYPE_FLOAT, 1, 0, 0, &ID_contrM);
 
     wfssize = (uint32_t *) malloc(sizeof(uint32_t) * 2);
     wfssize[0] = WFSsize;
     wfssize[1] = WFSsize;
-    ID_WFS = create_image_ID("cudatestwfs", 2, wfssize, _DATATYPE_FLOAT, 1, 0, 0);
+    create_image_ID("cudatestwfs", 2, wfssize, _DATATYPE_FLOAT, 1, 0, 0, &ID_WFS);
 
     cmdmodessize = (uint32_t *) malloc(sizeof(uint32_t) * 2);
     cmdmodessize[0] = NBmodes;
     cmdmodessize[1] = 1;
-    ID_cmd_modes = create_image_ID("cudatestcmd", 2, cmdmodessize, _DATATYPE_FLOAT,
-                                   1, 0, 0);
+    create_image_ID("cudatestcmd", 2, cmdmodessize, _DATATYPE_FLOAT,
+                    1, 0, 0, &ID_cmd_modes);
 
     GPU_loop_MultMat_setup(0, data.image[ID_contrM].name, data.image[ID_WFS].name,
                            data.image[ID_cmd_modes].name, GPUcnt, GPUdevices, 0, 1, 1, 0);