CudaStreamManager.cpp

//=======================================================================================
// ____          ____    __    ______     __________   __      __       __        __         
// \    \       |    |  |  |  |   _   \  |___    ___| |  |    |  |     /  \      |  |        
//  \    \      |    |  |  |  |  |_)   |     |  |     |  |    |  |    /    \     |  |        
//   \    \     |    |  |  |  |   _   /      |  |     |  |    |  |   /  /\  \    |  |        
//    \    \    |    |  |  |  |  | \  \      |  |     |   \__/   |  /  ____  \   |  |____    
//     \    \   |    |  |__|  |__|  \__\     |__|      \________/  /__/    \__\  |_______|   
//      \    \  |    |   ________________________________________________________________    
//       \    \ |    |  |  ______________________________________________________________|   
//        \    \|    |  |  |         __          __     __     __     ______      _______    
//         \         |  |  |_____   |  |        |  |   |  |   |  |   |   _  \    /  _____)   
//          \        |  |   _____|  |  |        |  |   |  |   |  |   |  | \  \   \_______    
//           \       |  |  |        |  |_____   |   \_/   |   |  |   |  |_/  /    _____  |
//            \ _____|  |__|        |________|   \_______/    |__|   |______/    (_______/   
//
//  This file is part of VirtualFluids. VirtualFluids is free software: you can 
//  redistribute it and/or modify it under the terms of the GNU General Public
//  License as published by the Free Software Foundation, either version 3 of 
//  the License, or (at your option) any later version.
//  
//  VirtualFluids is distributed in the hope that it will be useful, but WITHOUT 
//  ANY WARRANTY; without even the implied warranty of MERCHANTABILITY or 
//  FITNESS FOR A PARTICULAR PURPOSE.  See the GNU General Public License 
//  for more details.
//  
//  You should have received a copy of the GNU General Public License along
//  with VirtualFluids (see COPYING.txt). If not, see <http://www.gnu.org/licenses/>.
//
//=======================================================================================
#include "CudaStreamManager.h"
#include <helper_cuda.h>
#include <iostream>

CudaStreamManager::CudaStreamManager() {}

CudaStreamManager::~CudaStreamManager() {}

void CudaStreamManager::launchStreams(uint numberOfStreams)
{
    cudaStreams.resize(numberOfStreams);
    for (cudaStream_t &stream : cudaStreams)
        cudaStreamCreate(&stream);
}

void CudaStreamManager::terminateStreams()
{
    for (cudaStream_t &stream : cudaStreams)
        cudaStreamDestroy(stream);
}

cudaStream_t &CudaStreamManager::getStream(uint streamIndex)
{
    return cudaStreams[streamIndex]; }

void CudaStreamManager::createCudaEvents()
{
    checkCudaErrors(cudaEventCreateWithFlags(&startBulkKernel, cudaEventDisableTiming));
}

void CudaStreamManager::destroyCudaEvents() {checkCudaErrors(cudaEventDestroy(startBulkKernel));
}

void CudaStreamManager::triggerStartBulkKernel(int streamIndex)
{
    checkCudaErrors(cudaEventRecord(startBulkKernel, cudaStreams[streamIndex]));
}

void CudaStreamManager::triggerEventByName(std::string eventName, int streamIndex)
{
    if (eventName == "startBulkKernel")
        checkCudaErrors(cudaEventRecord(startBulkKernel, cudaStreams[streamIndex]));
    else
        std::cout << "unknown event name" << std::endl;
}

void CudaStreamManager::waitOnStartBulkKernelEvent(int streamIndex)
{
    checkCudaErrors(cudaStreamWaitEvent(cudaStreams[streamIndex], startBulkKernel));
}