Program Listing for File CudaCopyToOperation.cpp¶
↰ Return to documentation for file (umpire/op/CudaCopyToOperation.cpp
)
//////////////////////////////////////////////////////////////////////////////
// Copyright (c) 2018, Lawrence Livermore National Security, LLC.
// Produced at the Lawrence Livermore National Laboratory
//
// Created by David Beckingsale, david@llnl.gov
// LLNL-CODE-747640
//
// All rights reserved.
//
// This file is part of Umpire.
//
// For details, see https://github.com/LLNL/Umpire
// Please also see the LICENSE file for MIT license.
//////////////////////////////////////////////////////////////////////////////
#include "umpire/op/CudaCopyToOperation.hpp"
#include <cuda_runtime_api.h>
#include "umpire/util/Macros.hpp"
namespace umpire {
namespace op {
void CudaCopyToOperation::transform(
void* src_ptr,
void** dst_ptr,
umpire::util::AllocationRecord* UMPIRE_UNUSED_ARG(src_allocation),
umpire::util::AllocationRecord* UMPIRE_UNUSED_ARG(dst_allocation),
size_t length)
{
cudaError_t error =
::cudaMemcpy(*dst_ptr, src_ptr, length, cudaMemcpyHostToDevice);
if (error != cudaSuccess) {
UMPIRE_ERROR("cudaMemcpy( dest_ptr = " << *dst_ptr
<< ", src_ptr = " << src_ptr
<< ", length = " << length
<< ", cudaMemcpyHostToDevice ) failed with error: "
<< cudaGetErrorString(error));
}
UMPIRE_RECORD_STATISTIC(
"CudaCopyToOperation",
"src_ptr", reinterpret_cast<uintptr_t>(src_ptr),
"dst_ptr", reinterpret_cast<uintptr_t>(dst_ptr),
"size", length,
"event", "copy");
}
} // end of namespace op
} // end of namespace umpire