|
|
| cudaError_t cudaMemcpy2DFromArrayAsync |
( |
void * |
dst, |
|
|
size_t |
dpitch, |
|
|
const struct cudaArray * |
src, |
|
|
size_t |
wOffset, |
|
|
size_t |
hOffset, |
|
|
size_t |
width, |
|
|
size_t |
height, |
|
|
enum cudaMemcpyKind |
kind, |
|
|
cudaStream_t |
stream | |
|
) |
| | |
Copies a matrix (height rows of width bytes each) from the CUDA array srcArray starting at the upper left corner (wOffset, hOffset) to the memory area pointed to by dst, where kind is one of cudaMemcpyHostToHost, cudaMemcpyHostToDevice, cudaMemcpyDeviceToHost, or cudaMemcpyDeviceToDevice, and specifies the direction of the copy. dpitch is the width in memory in bytes of the 2D array pointed to by dst, including any padding added to the end of each row. cudaMemcpy2DFromArrayAsync() returns an error if dpitch is greater than the maximum allowed.
cudaMemcpy2DFromArrayAsync() is asynchronous with respect to the host, so the call may return before the copy is complete. It only works on page-locked host memory and returns an error if a pointer to pageable memory is passed as input. The copy can optionally be associated to a stream by passing a non-zero stream argument. If kind is cudaMemcpyHostToDevice or cudaMemcpyDeviceToHost and stream is non-zero, the copy may overlap with operations in other streams.
IMPORTANT NOTE: Copies with kind == cudaMemcpyDeviceToDevice are asynchronous with respect to the host, but never overlap with kernel execution.
- Parameters:
-
| dst | - Destination memory address |
| dpitch | - Pitch of destination memory |
| src | - Source memory address |
| wOffset | - Source starting X offset |
| hOffset | - Source starting Y offset |
| width | - Width of matrix transfer (columns in bytes) |
| height | - Height of matrix transfer (rows) |
| kind | - Type of transfer |
| stream | - Stream identifier |
- Returns:
- cudaSuccess, cudaErrorInvalidValue, cudaErrorInvalidDevicePointer, cudaErrorInvalidPitchValue, cudaErrorInvalidMemcpyDirection
- Note:
- Note that this function may also return error codes from previous, asynchronous launches.
- See also:
- cudaMemcpy, cudaMemcpy2D, cudaMemcpyToArray, cudaMemcpy2DToArray, cudaMemcpyFromArray, cudaMemcpy2DFromArray, cudaMemcpyArrayToArray, cudaMemcpy2DArrayToArray, cudaMemcpyToSymbol, cudaMemcpyFromSymbol, cudaMemcpyAsync, cudaMemcpy2DAsync, cudaMemcpyToArrayAsync, cudaMemcpy2DToArrayAsync, cudaMemcpyFromArrayAsync, cudaMemcpyToSymbolAsync, cudaMemcpyFromSymbolAsync
|
