|
hipError_t | hipMallocManaged (void **dev_ptr, size_t size, unsigned int flags __dparm(hipMemAttachGlobal)) |
| Allocates memory that will be automatically managed by AMD HMM. More...
|
|
hipError_t | hipMemPrefetchAsync (const void *dev_ptr, size_t count, int device, hipStream_t stream __dparm(0)) |
| Prefetches memory to the specified destination device using AMD HMM. More...
|
|
hipError_t | hipMemAdvise (const void *dev_ptr, size_t count, hipMemoryAdvise advice, int device) |
| Advise about the usage of a given memory range to AMD HMM. More...
|
|
hipError_t | hipMemRangeGetAttribute (void *data, size_t data_size, hipMemRangeAttribute attribute, const void *dev_ptr, size_t count) |
| Query an attribute of a given memory range in AMD HMM. More...
|
|
hipError_t | hipMemRangeGetAttributes (void **data, size_t *data_sizes, hipMemRangeAttribute *attributes, size_t num_attributes, const void *dev_ptr, size_t count) |
| Query attributes of a given memory range in AMD HMM. More...
|
|
hipError_t | hipStreamAttachMemAsync (hipStream_t stream, hipDeviceptr_t *dev_ptr, size_t length __dparm(0), unsigned int flags __dparm(hipMemAttachSingle)) |
| Attach memory to a stream asynchronously in AMD HMM. More...
|
|
This section describes the managed memory management functions of HIP runtime API.
◆ hipMallocManaged()
hipError_t hipMallocManaged |
( |
void ** |
dev_ptr, |
|
|
size_t |
size, |
|
|
unsigned int flags |
__dparmhipMemAttachGlobal |
|
) |
| |
◆ hipMemAdvise()
hipError_t hipMemAdvise |
( |
const void * |
dev_ptr, |
|
|
size_t |
count, |
|
|
hipMemoryAdvise |
advice, |
|
|
int |
device |
|
) |
| |
Advise about the usage of a given memory range to AMD HMM.
- Parameters
-
[in] | dev_ptr | pointer to memory to set the advice for |
[in] | count | size in bytes of the memory range |
[in] | advice | advice to be applied for the specified memory range |
[in] | device | device to apply the advice for |
- Returns
- hipSuccess, hipErrorInvalidValue
◆ hipMemPrefetchAsync()
hipError_t hipMemPrefetchAsync |
( |
const void * |
dev_ptr, |
|
|
size_t |
count, |
|
|
int |
device, |
|
|
hipStream_t stream |
__dparm0 |
|
) |
| |
Prefetches memory to the specified destination device using AMD HMM.
- Parameters
-
[in] | dev_ptr | pointer to be prefetched |
[in] | count | size in bytes for prefetching |
[in] | device | destination device to prefetch to |
[in] | stream | stream to enqueue prefetch operation |
- Returns
- hipSuccess, hipErrorInvalidValue
◆ hipMemRangeGetAttribute()
hipError_t hipMemRangeGetAttribute |
( |
void * |
data, |
|
|
size_t |
data_size, |
|
|
hipMemRangeAttribute |
attribute, |
|
|
const void * |
dev_ptr, |
|
|
size_t |
count |
|
) |
| |
Query an attribute of a given memory range in AMD HMM.
- Parameters
-
| [in/out] | data a pointer to a memory location where the result of each attribute query will be written to |
[in] | data_size | the size of data |
[in] | attribute | the attribute to query |
[in] | dev_ptr | start of the range to query |
[in] | count | size of the range to query |
- Returns
- hipSuccess, hipErrorInvalidValue
◆ hipMemRangeGetAttributes()
hipError_t hipMemRangeGetAttributes |
( |
void ** |
data, |
|
|
size_t * |
data_sizes, |
|
|
hipMemRangeAttribute * |
attributes, |
|
|
size_t |
num_attributes, |
|
|
const void * |
dev_ptr, |
|
|
size_t |
count |
|
) |
| |
Query attributes of a given memory range in AMD HMM.
- Parameters
-
| [in/out] | data a two-dimensional array containing pointers to memory locations where the result of each attribute query will be written to |
[in] | data_sizes | an array, containing the sizes of each result |
[in] | attributes | the attribute to query |
[in] | num_attributes | an array of attributes to query (numAttributes and the number of attributes in this array should match) |
[in] | dev_ptr | start of the range to query |
[in] | count | size of the range to query |
- Returns
- hipSuccess, hipErrorInvalidValue
◆ hipStreamAttachMemAsync()
hipError_t hipStreamAttachMemAsync |
( |
hipStream_t |
stream, |
|
|
hipDeviceptr_t * |
dev_ptr, |
|
|
size_t length |
__dparm0, |
|
|
unsigned int flags |
__dparmhipMemAttachSingle |
|
) |
| |
Attach memory to a stream asynchronously in AMD HMM.
- Parameters
-
[in] | stream | - stream in which to enqueue the attach operation |
[in] | dev_ptr | - pointer to memory (must be a pointer to managed memory or to a valid host-accessible region of system-allocated memory) |
[in] | length | - length of memory (defaults to zero) |
[in] | flags | - must be one of cudaMemAttachGlobal, cudaMemAttachHost or cudaMemAttachSingle (defaults to cudaMemAttachSingle) |
- Returns
- hipSuccess, hipErrorInvalidValue