Home
last modified time | relevance | path

Searched refs:d_array (Results 1 – 9 of 9) sorted by relevance

/libCEED/backends/cuda-ref/
H A Dceed-cuda-ref-vector.c32 *need_sync = has_valid_array && !impl->d_array; in CeedVectorNeedSync_Cuda()
53 impl->d_array = impl->d_array_borrowed; in CeedVectorSyncH2D_Cuda()
55 impl->d_array = impl->d_array_owned; in CeedVectorSyncH2D_Cuda()
58 impl->d_array = impl->d_array_owned; in CeedVectorSyncH2D_Cuda()
60 …CeedCallCuda(CeedVectorReturnCeed(vec), cudaMemcpy(impl->d_array, impl->h_array, bytes, cudaMemcpy… in CeedVectorSyncH2D_Cuda()
73 …CeedCheck(impl->d_array, CeedVectorReturnCeed(vec), CEED_ERROR_BACKEND, "No valid device data to s… in CeedVectorSyncD2H_Cuda()
90 …CeedCallCuda(CeedVectorReturnCeed(vec), cudaMemcpy(impl->h_array, impl->d_array, bytes, cudaMemcpy… in CeedVectorSyncD2H_Cuda()
121 impl->d_array = NULL; in CeedVectorSetAllInvalid_Cuda()
132 *has_valid_array = impl->h_array || impl->d_array; in CeedVectorHasValidArray_Cuda()
200 … (const CeedScalar **)&impl->d_array_borrowed, (const CeedScalar **)&impl->d_array)); in CeedVectorSetArrayDevice_Cuda()
[all …]
H A Dceed-cuda-ref.h19 CeedScalar *d_array; member
/libCEED/backends/hip-ref/
H A Dceed-hip-ref-vector.c32 *need_sync = has_valid_array && !impl->d_array; in CeedVectorNeedSync_Hip()
53 impl->d_array = impl->d_array_borrowed; in CeedVectorSyncH2D_Hip()
55 impl->d_array = impl->d_array_owned; in CeedVectorSyncH2D_Hip()
58 impl->d_array = impl->d_array_owned; in CeedVectorSyncH2D_Hip()
60 …CeedCallHip(CeedVectorReturnCeed(vec), hipMemcpy(impl->d_array, impl->h_array, bytes, hipMemcpyHos… in CeedVectorSyncH2D_Hip()
74 …CeedCheck(impl->d_array, CeedVectorReturnCeed(vec), CEED_ERROR_BACKEND, "No valid device data to s… in CeedVectorSyncD2H_Hip()
90 …CeedCallHip(CeedVectorReturnCeed(vec), hipMemcpy(impl->h_array, impl->d_array, bytes, hipMemcpyDev… in CeedVectorSyncD2H_Hip()
129 impl->d_array = NULL; in CeedVectorSetAllInvalid_Hip()
140 *has_valid_array = impl->h_array || impl->d_array; in CeedVectorHasValidArray_Hip()
212 … (const CeedScalar **)&impl->d_array_borrowed, (const CeedScalar **)&impl->d_array)); in CeedVectorSetArrayDevice_Hip()
[all …]
H A Dceed-hip-ref.h24 CeedScalar *d_array; member
/libCEED/backends/sycl-ref/
H A Dceed-sycl-vector.sycl.cpp31 *need_sync = has_valid_array && !impl->d_array; in CeedVectorNeedSync_Sycl()
54 impl->d_array = impl->d_array_borrowed; in CeedVectorSyncH2D_Sycl()
56 impl->d_array = impl->d_array_owned; in CeedVectorSyncH2D_Sycl()
59 impl->d_array = impl->d_array_owned; in CeedVectorSyncH2D_Sycl()
66 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(impl->h_array, impl->d_array, length, e).wait… in CeedVectorSyncH2D_Sycl()
84 CeedCheck(impl->d_array, ceed, CEED_ERROR_BACKEND, "No valid device data to sync to host"); in CeedVectorSyncD2H_Sycl()
100 …CeedCallSycl(ceed, data->sycl_queue.copy<CeedScalar>(impl->d_array, impl->h_array, length, e).wait… in CeedVectorSyncD2H_Sycl()
132 impl->d_array = NULL; in CeedVectorSetAllInvalid_Sycl()
143 *has_valid_array = impl->h_array || impl->d_array; in CeedVectorHasValidArray_Sycl()
227 impl->d_array = impl->d_array_owned; in CeedVectorSetArrayDevice_Sycl()
[all …]
H A Dceed-sycl-ref.hpp22 CeedScalar *d_array; member
/libCEED/backends/cuda-ref/kernels/
H A Dcuda-ref-vector.cu25 extern "C" int CeedDeviceCopyStrided_Cuda(CeedScalar *d_array, CeedSize start, CeedSize stop, CeedS… in CeedDeviceCopyStrided_Cuda() argument
31 copyStridedK<<<grid_size, block_size>>>(d_array, start, stop, step, d_copy_array); in CeedDeviceCopyStrided_Cuda()
47 extern "C" int CeedDeviceSetValue_Cuda(CeedScalar *d_array, CeedSize length, CeedScalar val) { in CeedDeviceSetValue_Cuda() argument
53 setValueK<<<grid_size, block_size>>>(d_array, length, val); in CeedDeviceSetValue_Cuda()
71 extern "C" int CeedDeviceSetValueStrided_Cuda(CeedScalar *d_array, CeedSize start, CeedSize stop, C… in CeedDeviceSetValueStrided_Cuda() argument
77 setValueStridedK<<<grid_size, block_size>>>(d_array, start, stop, step, val); in CeedDeviceSetValueStrided_Cuda()
95 extern "C" int CeedDeviceReciprocal_Cuda(CeedScalar *d_array, CeedSize length) { in CeedDeviceReciprocal_Cuda() argument
101 rcpValueK<<<grid_size, block_size>>>(d_array, length); in CeedDeviceReciprocal_Cuda()
/libCEED/backends/hip-ref/kernels/
H A Dhip-ref-vector.hip.cpp25 extern "C" int CeedDeviceCopyStrided_Hip(CeedScalar *d_array, CeedSize start, CeedSize step, CeedSi… in CeedDeviceCopyStrided_Hip() argument
31 …hipLaunchKernelGGL(copyStridedK, dim3(grid_size), dim3(block_size), 0, 0, d_array, start, step, le… in CeedDeviceCopyStrided_Hip()
47 extern "C" int CeedDeviceSetValue_Hip(CeedScalar *d_array, CeedSize length, CeedScalar val) { in CeedDeviceSetValue_Hip() argument
53 hipLaunchKernelGGL(setValueK, dim3(grid_size), dim3(block_size), 0, 0, d_array, length, val); in CeedDeviceSetValue_Hip()
71 extern "C" int CeedDeviceSetValueStrided_Hip(CeedScalar *d_array, CeedSize start, CeedInt stop, Cee… in CeedDeviceSetValueStrided_Hip() argument
77 …hipLaunchKernelGGL(setValueStridedK, dim3(grid_size), dim3(block_size), 0, 0, d_array, start, stop… in CeedDeviceSetValueStrided_Hip()
95 extern "C" int CeedDeviceReciprocal_Hip(CeedScalar *d_array, CeedSize length) { in CeedDeviceReciprocal_Hip() argument
101 hipLaunchKernelGGL(rcpValueK, dim3(grid_size), dim3(block_size), 0, 0, d_array, length); in CeedDeviceReciprocal_Hip()
/libCEED/backends/sycl-ref/kernels/
H A Dsycl-ref-vector.cpp25 extern "C" int CeedDeviceSetValue_Sycl(CeedScalar *d_array, CeedInt length, CeedScalar val) { in CeedDeviceSetValue_Sycl() argument
31 setValueK<<<grid_size, block_size>>>(d_array, length, val); in CeedDeviceSetValue_Sycl()
48 extern "C" int CeedDeviceReciprocal_Sycl(CeedScalar *d_array, CeedInt length) { in CeedDeviceReciprocal_Sycl() argument
54 rcpValueK<<<grid_size, block_size>>>(d_array, length); in CeedDeviceReciprocal_Sycl()