Lines Matching refs:d_data
32 impl->d_data = impl->d_data_borrowed; in CeedQFunctionContextSyncH2D_Cuda()
34 impl->d_data = impl->d_data_owned; in CeedQFunctionContextSyncH2D_Cuda()
37 impl->d_data = impl->d_data_owned; in CeedQFunctionContextSyncH2D_Cuda()
39 CeedCallCuda(ceed, cudaMemcpy(impl->d_data, impl->h_data, ctx_size, cudaMemcpyHostToDevice)); in CeedQFunctionContextSyncH2D_Cuda()
55 CeedCheck(impl->d_data, ceed, CEED_ERROR_BACKEND, "No valid device data to sync to host"); in CeedQFunctionContextSyncD2H_Cuda()
67 CeedCallCuda(ceed, cudaMemcpy(impl->h_data, impl->d_data, ctx_size, cudaMemcpyDeviceToHost)); in CeedQFunctionContextSyncD2H_Cuda()
93 impl->d_data = NULL; in CeedQFunctionContextSetAllInvalid_Cuda()
104 *has_valid_data = impl && (impl->h_data || impl->d_data); in CeedQFunctionContextHasValidData_Cuda()
141 *need_sync = has_valid_data && !impl->d_data; in CeedQFunctionContextNeedSync_Cuda()
196 impl->d_data = impl->d_data_owned; in CeedQFunctionContextSetDataDevice_Cuda()
197 CeedCallCuda(ceed, cudaMemcpy(impl->d_data, data, ctx_size, cudaMemcpyDeviceToDevice)); in CeedQFunctionContextSetDataDevice_Cuda()
202 impl->d_data = data; in CeedQFunctionContextSetDataDevice_Cuda()
207 impl->d_data = data; in CeedQFunctionContextSetDataDevice_Cuda()
252 impl->d_data = NULL; in CeedQFunctionContextTakeData_Cuda()
278 *(void **)data = impl->d_data; in CeedQFunctionContextGetDataCore_Cuda()
307 impl->d_data = *(void **)data; in CeedQFunctionContextGetData_Cuda()