@@ -36,7 +36,7 @@ enum nixl_gpu_coordination_level_t {
36
36
37
37
/* *
38
38
* @brief Post a memory transfer request to the GPU.
39
- *
39
+ *
40
40
* @param req_hndl [in] The request handle.
41
41
* @param address [in] The local address of the memory to be transferred.
42
42
* @param remote_addr [in] The remote address of the memory to be transferred.
@@ -45,10 +45,10 @@ enum nixl_gpu_coordination_level_t {
45
45
*
46
46
* @return nixl_status_t Error code if call was not successful
47
47
*/
48
- template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
49
- __device__ static inline nixl_status_t
50
- nixlGpuPostMemXferReq (nixlGpuXferReqH* req_hndl,
51
- void *address,
48
+ template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
49
+ __device__ static inline nixl_status_t
50
+ nixlGpuPostMemXferReq (nixlGpuXferReqH* req_hndl,
51
+ void *address,
52
52
uint64_t remote_addr,
53
53
nixlGpuXferStatusH* xfer_status = nullptr ,
54
54
bool is_no_delay = true )
@@ -58,7 +58,7 @@ nixlGpuPostMemXferReq(nixlGpuXferReqH* req_hndl,
58
58
59
59
/* *
60
60
* @brief Post a signal transfer request to the GPU.
61
- *
61
+ *
62
62
* @param req_hndl [in] The request handle.
63
63
* @param signal_inc [in] The increment of the signal.
64
64
* @param signal_remote_addr [in] The remote address of the signal.
@@ -67,25 +67,25 @@ nixlGpuPostMemXferReq(nixlGpuXferReqH* req_hndl,
67
67
*
68
68
* @return nixl_status_t Error code if call was not successful
69
69
*/
70
- template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
71
- __device__ static inline nixl_status_t
72
- nixlGpuPostSignalXferReq (nixlGpuXferReqH* req_hndl,
73
- uint64_t signal_inc,
74
- uint64_t signal_remote_addr,
75
- nixlGpuXferStatusH* xfer_status = nullptr ,
70
+ template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
71
+ __device__ static inline nixl_status_t
72
+ nixlGpuPostSignalXferReq (nixlGpuXferReqH* req_hndl,
73
+ uint64_t signal_inc,
74
+ uint64_t signal_remote_addr,
75
+ nixlGpuXferStatusH* xfer_status = nullptr ,
76
76
bool is_no_delay = true )
77
77
{
78
78
return NIXL_ERR_NOT_SUPPORTED;
79
79
}
80
80
81
81
/* *
82
82
* @brief Post a partial memory transfer request to the GPU.
83
- *
83
+ *
84
84
* @param req_hndl [in] The request handle.
85
85
* @param count [in] The number of blocks to send.
86
86
* @param indices [in] The indices of the blocks to send.
87
87
* @param sizes [in] The sizes of the blocks to send.
88
- * @param addreses [in] The addresses of the blocks to send.
88
+ * @param addresses [in] The addresses of the blocks to send.
89
89
* @param remote_addrs [in] The remote addresses of the blocks to send.
90
90
* @param signal_remote_addr [in] The remote address of the signal. If address is 0, no signal.
91
91
* @param signal_inc [in] The increment of the signal.
@@ -94,28 +94,28 @@ nixlGpuPostSignalXferReq(nixlGpuXferReqH* req_hndl,
94
94
*
95
95
* @return nixl_status_t Error code if call was not successful
96
96
*/
97
- template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
98
- __device__ static inline nixl_status_t
99
- nixlGpuPostPartialMemXferReq (nixlGpuXferReqH* req_hndl,
100
- size_t count,
97
+ template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
98
+ __device__ static inline nixl_status_t
99
+ nixlGpuPostPartialMemXferReq (nixlGpuXferReqH* req_hndl,
100
+ size_t count,
101
101
const int * indices,
102
- const size_t * sizes,
103
- const void ** addreses,
104
- const uint64_t * remote_addrs,
102
+ const size_t * sizes,
103
+ const void ** addresses,
104
+ const uint64_t * remote_addrs,
105
105
uint64_t signal_remote_addr,
106
- uint64_t signal_inc,
107
- nixlGpuXferStatusH* xfer_status = nullptr ,
106
+ uint64_t signal_inc,
107
+ nixlGpuXferStatusH* xfer_status = nullptr ,
108
108
bool is_no_delay = true )
109
109
{
110
110
return NIXL_ERR_NOT_SUPPORTED;
111
111
}
112
112
113
113
/* *
114
114
* @brief Post a memory transfer request to the GPU.
115
- *
115
+ *
116
116
* @param req_hndl [in] The request handle.
117
117
* @param sizes [in] The sizes of the blocks to send.
118
- * @param addreses [in] The addresses of the blocks to send.
118
+ * @param addresses [in] The addresses of the blocks to send.
119
119
* @param remote_addrs [in] The remote addresses of the blocks to send.
120
120
* @param signal_remote_addr [in] The remote address of the signal. If address is 0, no signal.
121
121
* @param signal_inc [in] The increment of the signal.
@@ -124,29 +124,29 @@ nixlGpuPostPartialMemXferReq(nixlGpuXferReqH* req_hndl,
124
124
*
125
125
* @return nixl_status_t Error code if call was not successful
126
126
*/
127
- template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
128
- __device__ static inline nixl_status_t
129
- nixlPostGpuXferReq (nixlGpuXferReqH* req_hndl,
130
- const size_t * sizes,
131
- const void ** addreses,
132
- const uint64_t * remote_addrs,
127
+ template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
128
+ __device__ static inline nixl_status_t
129
+ nixlPostGpuXferReq (nixlGpuXferReqH* req_hndl,
130
+ const size_t * sizes,
131
+ const void ** addresses,
132
+ const uint64_t * remote_addrs,
133
133
uint64_t signal_remote_addr,
134
- uint64_t signal_inc,
135
- nixlGpuXferStatusH* xfer_status = nullptr ,
136
- bool is_no_delay = true )
134
+ uint64_t signal_inc,
135
+ nixlGpuXferStatusH* xfer_status = nullptr ,
136
+ bool is_no_delay = true )
137
137
{
138
138
return NIXL_ERR_NOT_SUPPORTED;
139
139
}
140
140
141
141
/* *
142
142
* @brief Get the status of a transfer request.
143
- *
143
+ *
144
144
* @param xfer_status [in] The status of the transfer.
145
145
*
146
146
* @return nixl_status_t Error code if call was not successful
147
147
*/
148
- template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
149
- __device__ static inline nixl_status_t
148
+ template <nixl_gpu_coordination_level_t level = NIXL_GPU_COORDINATION_BLOCK>
149
+ __device__ static inline nixl_status_t
150
150
nixlGpuGetXferStatus (nixlGpuXferStatusH* xfer_status)
151
151
{
152
152
return NIXL_ERR_NOT_SUPPORTED;
0 commit comments