sdashmiz
fcfa0d0733
- hipArray will be an internal struct from rocm6.0
Signed-off-by: sdashmiz <shadi.dashmiz@amd.com>
Change-Id: Icf97fe96b87be8532098cd7f9ceaad099f99c9b9
[ROCm/clr commit: c089ef4a2b]
117 lines
6.9 KiB
C++
117 lines
6.9 KiB
C++
/*
|
|
Copyright (c) 2023 Advanced Micro Devices, Inc. All rights reserved.
|
|
|
|
Permission is hereby granted, free of charge, to any person obtaining a copy
|
|
of this software and associated documentation files (the "Software"), to deal
|
|
in the Software without restriction, including without limitation the rights
|
|
to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
|
|
copies of the Software, and to permit persons to whom the Software is
|
|
furnished to do so, subject to the following conditions:
|
|
|
|
The above copyright notice and this permission notice shall be included in
|
|
all copies or substantial portions of the Software.
|
|
|
|
THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
|
|
IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
|
|
FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT. IN NO EVENT SHALL THE
|
|
AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
|
|
LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
|
|
OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
|
|
THE SOFTWARE.
|
|
*/
|
|
|
|
#include "hip_conversions.hpp"
|
|
|
|
hipError_t ihipMemcpy3D_validate(const hipMemcpy3DParms* p);
|
|
|
|
hipError_t ihipMemcpy_validate(void* dst, const void* src, size_t sizeBytes, hipMemcpyKind kind);
|
|
|
|
hipError_t ihipMemcpyCommand(amd::Command*& command, void* dst, const void* src, size_t sizeBytes,
|
|
hipMemcpyKind kind, hip::Stream& stream, bool isAsync = false);
|
|
|
|
void ihipHtoHMemcpy(void* dst, const void* src, size_t sizeBytes, hip::Stream& stream);
|
|
|
|
bool IsHtoHMemcpy(void* dst, const void* src, hipMemcpyKind kind);
|
|
|
|
hipError_t ihipLaunchKernel_validate(hipFunction_t f, uint32_t globalWorkSizeX,
|
|
uint32_t globalWorkSizeY, uint32_t globalWorkSizeZ,
|
|
uint32_t blockDimX, uint32_t blockDimY, uint32_t blockDimZ,
|
|
uint32_t sharedMemBytes, void** kernelParams, void** extra,
|
|
int deviceId, uint32_t params);
|
|
|
|
hipError_t ihipMemset_validate(void* dst, int64_t value, size_t valueSize, size_t sizeBytes);
|
|
|
|
hipError_t ihipMemset3D_validate(hipPitchedPtr pitchedDevPtr, int value, hipExtent extent,
|
|
size_t sizeBytes);
|
|
|
|
hipError_t ihipLaunchKernelCommand(amd::Command*& command, hipFunction_t f,
|
|
uint32_t globalWorkSizeX, uint32_t globalWorkSizeY,
|
|
uint32_t globalWorkSizeZ, uint32_t blockDimX, uint32_t blockDimY,
|
|
uint32_t blockDimZ, uint32_t sharedMemBytes,
|
|
hip::Stream* stream, void** kernelParams, void** extra,
|
|
hipEvent_t startEvent, hipEvent_t stopEvent, uint32_t flags,
|
|
uint32_t params, uint32_t gridId, uint32_t numGrids,
|
|
uint64_t prevGridSum, uint64_t allGridSum, uint32_t firstDevice);
|
|
|
|
hipError_t ihipMemcpy3DCommand(amd::Command*& command, const hipMemcpy3DParms* p,
|
|
hip::Stream* stream);
|
|
|
|
hipError_t ihipMemsetCommand(std::vector<amd::Command*>& commands, void* dst, int64_t value,
|
|
size_t valueSize, size_t sizeBytes, hip::Stream* stream);
|
|
|
|
hipError_t ihipMemset3DCommand(std::vector<amd::Command*>& commands, hipPitchedPtr pitchedDevPtr,
|
|
int value, hipExtent extent, hip::Stream* stream, size_t elementSize = 1);
|
|
|
|
hipError_t ihipMemcpySymbol_validate(const void* symbol, size_t sizeBytes, size_t offset,
|
|
size_t& sym_size, hipDeviceptr_t& device_ptr);
|
|
|
|
hipError_t ihipMemcpyAtoDValidate(hipArray_t srcArray, void* dstDevice, amd::Coord3D& srcOrigin,
|
|
amd::Coord3D& dstOrigin, amd::Coord3D& copyRegion,
|
|
size_t dstRowPitch, size_t dstSlicePitch, amd::Memory*& dstMemory,
|
|
amd::Image*& srcImage, amd::BufferRect& srcRect,
|
|
amd::BufferRect& dstRect);
|
|
|
|
hipError_t ihipMemcpyDtoAValidate(void* srcDevice, hipArray_t dstArray, amd::Coord3D& srcOrigin,
|
|
amd::Coord3D& dstOrigin, amd::Coord3D& copyRegion,
|
|
size_t srcRowPitch, size_t srcSlicePitch, amd::Image*& dstImage,
|
|
amd::Memory*& srcMemory, amd::BufferRect& dstRect,
|
|
amd::BufferRect& srcRect);
|
|
|
|
hipError_t ihipMemcpyDtoDValidate(void* srcDevice, void* dstDevice, amd::Coord3D& srcOrigin,
|
|
amd::Coord3D& dstOrigin, amd::Coord3D& copyRegion,
|
|
size_t srcRowPitch, size_t srcSlicePitch, size_t dstRowPitch,
|
|
size_t dstSlicePitch, amd::Memory*& srcMemory,
|
|
amd::Memory*& dstMemory, amd::BufferRect& srcRect,
|
|
amd::BufferRect& dstRect);
|
|
|
|
|
|
hipError_t ihipMemcpyDtoHValidate(void* srcDevice, void* dstHost, amd::Coord3D& srcOrigin,
|
|
amd::Coord3D& dstOrigin, amd::Coord3D& copyRegion,
|
|
size_t srcRowPitch, size_t srcSlicePitch, size_t dstRowPitch,
|
|
size_t dstSlicePitch, amd::Memory*& srcMemory,
|
|
amd::BufferRect& srcRect, amd::BufferRect& dstRect);
|
|
|
|
hipError_t ihipMemcpyHtoDValidate(const void* srcHost, void* dstDevice, amd::Coord3D& srcOrigin,
|
|
amd::Coord3D& dstOrigin, amd::Coord3D& copyRegion,
|
|
size_t srcRowPitch, size_t srcSlicePitch, size_t dstRowPitch,
|
|
size_t dstSlicePitch, amd::Memory*& dstMemory,
|
|
amd::BufferRect& srcRect, amd::BufferRect& dstRect);
|
|
|
|
|
|
hipError_t ihipMemcpyAtoAValidate(hipArray_t srcArray, hipArray_t dstArray, amd::Coord3D& srcOrigin,
|
|
amd::Coord3D& dstOrigin, amd::Coord3D& copyRegion,
|
|
amd::Image*& srcImage, amd::Image*& dstImage);
|
|
|
|
|
|
hipError_t ihipMemcpyHtoAValidate(const void* srcHost, hipArray_t dstArray, amd::Coord3D& srcOrigin,
|
|
amd::Coord3D& dstOrigin, amd::Coord3D& copyRegion,
|
|
size_t srcRowPitch, size_t srcSlicePitch, amd::Image*& dstImage,
|
|
amd::BufferRect& srcRect);
|
|
|
|
hipError_t ihipMemcpyAtoHValidate(hipArray_t srcArray, void* dstHost, amd::Coord3D& srcOrigin,
|
|
amd::Coord3D& dstOrigin, amd::Coord3D& copyRegion,
|
|
size_t dstRowPitch, size_t dstSlicePitch, amd::Image*& srcImage,
|
|
amd::BufferRect& dstRect);
|
|
|
|
hipError_t ihipGraphMemsetParams_validate(const hipMemsetParams* pNodeParams);
|