Enabled copying summationPoints_ from and to device

Author: Divya Kamath

Simulator/Vertices/Neuro/AllSpikingNeurons.cpp

@@ -20,15 +20,7 @@ void AllSpikingNeurons::setupVertices()
 
    hasFired_.assign(size_, false);
    vertexEvents_.assign(size_, maxSpikes);
-#if defined(USE_GPU)
-   // We don't allocate memory for summationPoints_ in CPU when building the GPU
-   // implementation. This is to avoid misusing it in GPU code.
-   // summationPoints_ = nullptr;
-
-#else
    summationPoints_.assign(size_, 0);
-
-#endif
 }
 
 ///  Register spike history variables for all neurons.

Simulator/Vertices/Neuro/AllSpikingNeurons_d.cpp

@@ -84,6 +84,9 @@ void AllSpikingNeurons::copyToDevice(void *deviceAddress)
       HANDLE_ERROR(cudaMemcpy(pSpikeHistory[i], vertexEvents_[i].dataSeries_.data(),
                               maxSpikes * sizeof(uint64_t), cudaMemcpyHostToDevice));
    }
+
+   HANDLE_ERROR(cudaMemcpy(allVerticesDevice.summationPoints_, summationPoints_.data(),
+                           count * sizeof(BGFLOAT), cudaMemcpyHostToDevice));
 }
 void AllSpikingNeurons::copyFromDevice(void *deviceAddress)
 {
@@ -141,6 +144,9 @@ void AllSpikingNeurons::copyFromDevice(void *deviceAddress)
       HANDLE_ERROR(cudaMemcpy(vertexEvents_[i].dataSeries_.data(), pSpikeHistory[i],
                               maxSpikes * sizeof(uint64_t *), cudaMemcpyDeviceToHost));
    }
+
+   HANDLE_ERROR(cudaMemcpy(summationPoints_.data(), allVerticesDevice.summationPoints_,
+                           numVertices * sizeof(BGFLOAT), cudaMemcpyDeviceToHost));
 }
 
 ///  Clear the spike counts out of all neurons in device memory.