Lines Matching refs:impl
29 CeedElemRestriction_Cuda *impl; in CeedElemRestrictionSetupCompile_Cuda() local
31 CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl)); in CeedElemRestrictionSetupCompile_Cuda()
42 is_deterministic = impl->d_l_vec_indices != NULL; in CeedElemRestrictionSetupCompile_Cuda()
55 …CeedCallBackend(CeedCompile_Cuda(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZ… in CeedElemRestrictionSetupCompile_Cuda()
58 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "StridedNoTranspose", &impl->ApplyNoTranspo… in CeedElemRestrictionSetupCompile_Cuda()
59 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "StridedTranspose", &impl->ApplyTranspose)); in CeedElemRestrictionSetupCompile_Cuda()
64 …CeedCallBackend(CeedCompile_Cuda(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZ… in CeedElemRestrictionSetupCompile_Cuda()
65 … "RSTR_NUM_COMP", num_comp, "RSTR_NUM_NODES", impl->num_nodes, "RSTR_COMP_STRIDE", comp_stride, in CeedElemRestrictionSetupCompile_Cuda()
67 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OffsetNoTranspose", &impl->ApplyNoTranspos… in CeedElemRestrictionSetupCompile_Cuda()
68 … CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OffsetTranspose", &impl->ApplyTranspose)); in CeedElemRestrictionSetupCompile_Cuda()
75 …CeedCallBackend(CeedCompile_Cuda(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZ… in CeedElemRestrictionSetupCompile_Cuda()
76 … "RSTR_NUM_COMP", num_comp, "RSTR_NUM_NODES", impl->num_nodes, "RSTR_COMP_STRIDE", comp_stride, in CeedElemRestrictionSetupCompile_Cuda()
78 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OffsetNoTranspose", &impl->ApplyNoTranspos… in CeedElemRestrictionSetupCompile_Cuda()
79 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "AtPointsTranspose", &impl->ApplyTranspose)… in CeedElemRestrictionSetupCompile_Cuda()
86 …CeedCallBackend(CeedCompile_Cuda(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZ… in CeedElemRestrictionSetupCompile_Cuda()
87 … "RSTR_NUM_COMP", num_comp, "RSTR_NUM_NODES", impl->num_nodes, "RSTR_COMP_STRIDE", comp_stride, in CeedElemRestrictionSetupCompile_Cuda()
89 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OrientedNoTranspose", &impl->ApplyNoTransp… in CeedElemRestrictionSetupCompile_Cuda()
90 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OffsetNoTranspose", &impl->ApplyUnsignedNo… in CeedElemRestrictionSetupCompile_Cuda()
91 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OrientedTranspose", &impl->ApplyTranspose)… in CeedElemRestrictionSetupCompile_Cuda()
92 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OffsetTranspose", &impl->ApplyUnsignedTran… in CeedElemRestrictionSetupCompile_Cuda()
98 …CeedCallBackend(CeedCompile_Cuda(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZ… in CeedElemRestrictionSetupCompile_Cuda()
99 … "RSTR_NUM_COMP", num_comp, "RSTR_NUM_NODES", impl->num_nodes, "RSTR_COMP_STRIDE", comp_stride, in CeedElemRestrictionSetupCompile_Cuda()
101 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "CurlOrientedNoTranspose", &impl->ApplyNoTr… in CeedElemRestrictionSetupCompile_Cuda()
102 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "CurlOrientedUnsignedNoTranspose", &impl->A… in CeedElemRestrictionSetupCompile_Cuda()
103 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OffsetNoTranspose", &impl->ApplyUnoriented… in CeedElemRestrictionSetupCompile_Cuda()
104 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "CurlOrientedTranspose", &impl->ApplyTransp… in CeedElemRestrictionSetupCompile_Cuda()
105 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "CurlOrientedUnsignedTranspose", &impl->App… in CeedElemRestrictionSetupCompile_Cuda()
106 …CeedCallBackend(CeedGetKernel_Cuda(ceed, impl->module, "OffsetTranspose", &impl->ApplyUnorientedTr… in CeedElemRestrictionSetupCompile_Cuda()
122 CeedElemRestriction_Cuda *impl; in CeedElemRestrictionApply_Cuda_Core() local
124 CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl)); in CeedElemRestrictionApply_Cuda_Core()
129 if (!impl->module) { in CeedElemRestrictionApply_Cuda_Core()
150 const CeedInt grid = CeedDivUpInt(impl->num_nodes, block_size); in CeedElemRestrictionApply_Cuda_Core()
156 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyNoTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
160 void *args[] = {&impl->d_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
162 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyNoTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
166 void *args[] = {&impl->d_offsets, &impl->d_orients, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
168 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyNoTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
170 void *args[] = {&impl->d_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
172 … CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnsignedNoTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
177 void *args[] = {&impl->d_offsets, &impl->d_curl_orients, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
179 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyNoTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
181 void *args[] = {&impl->d_offsets, &impl->d_curl_orients, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
183 … CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnsignedNoTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
185 void *args[] = {&impl->d_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
187 …CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnorientedNoTranspose, grid, block_size, args)… in CeedElemRestrictionApply_Cuda_Core()
193 const bool is_deterministic = impl->d_l_vec_indices != NULL; in CeedElemRestrictionApply_Cuda_Core()
195 const CeedInt grid = CeedDivUpInt(impl->num_nodes, block_size); in CeedElemRestrictionApply_Cuda_Core()
201 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
205 void *args[] = {&impl->d_offsets, &impl->d_points_per_elem, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
207 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
209 …void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_points_per_elem, &impl->d_t_o… in CeedElemRestrictionApply_Cuda_Core()
211 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
216 void *args[] = {&impl->d_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
218 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
220 … void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
222 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
228 void *args[] = {&impl->d_offsets, &impl->d_orients, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
230 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
232 …void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &impl->d_orients, … in CeedElemRestrictionApply_Cuda_Core()
234 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
238 void *args[] = {&impl->d_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
240 … CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnsignedTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
242 … void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
244 … CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnsignedTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
251 void *args[] = {&impl->d_offsets, &impl->d_curl_orients, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
253 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
255 …void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &impl->d_curl_orie… in CeedElemRestrictionApply_Cuda_Core()
257 CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
261 void *args[] = {&impl->d_offsets, &impl->d_curl_orients, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
263 … CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnsignedTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
265 …void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &impl->d_curl_orie… in CeedElemRestrictionApply_Cuda_Core()
267 … CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnsignedTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
271 void *args[] = {&impl->d_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
273 … CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnorientedTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
275 … void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &d_u, &d_v}; in CeedElemRestrictionApply_Cuda_Core()
277 … CeedCallBackend(CeedRunKernel_Cuda(ceed, impl->ApplyUnorientedTranspose, grid, block_size, args)); in CeedElemRestrictionApply_Cuda_Core()
320 CeedElemRestriction_Cuda *impl; in CeedElemRestrictionGetOffsets_Cuda() local
323 CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl)); in CeedElemRestrictionGetOffsets_Cuda()
327 *offsets = rstr_type == CEED_RESTRICTION_POINTS ? impl->h_offsets_at_points : impl->h_offsets; in CeedElemRestrictionGetOffsets_Cuda()
330 *offsets = rstr_type == CEED_RESTRICTION_POINTS ? impl->d_offsets_at_points : impl->d_offsets; in CeedElemRestrictionGetOffsets_Cuda()
340 CeedElemRestriction_Cuda *impl; in CeedElemRestrictionGetOrientations_Cuda() local
341 CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl)); in CeedElemRestrictionGetOrientations_Cuda()
345 *orients = impl->h_orients; in CeedElemRestrictionGetOrientations_Cuda()
348 *orients = impl->d_orients; in CeedElemRestrictionGetOrientations_Cuda()
358 CeedElemRestriction_Cuda *impl; in CeedElemRestrictionGetCurlOrientations_Cuda() local
359 CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl)); in CeedElemRestrictionGetCurlOrientations_Cuda()
363 *curl_orients = impl->h_curl_orients; in CeedElemRestrictionGetCurlOrientations_Cuda()
366 *curl_orients = impl->d_curl_orients; in CeedElemRestrictionGetCurlOrientations_Cuda()
388 CeedElemRestriction_Cuda *impl; in CeedElemRestrictionDestroy_Cuda() local
390 CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl)); in CeedElemRestrictionDestroy_Cuda()
392 if (impl->module) { in CeedElemRestrictionDestroy_Cuda()
393 CeedCallCuda(ceed, cuModuleUnload(impl->module)); in CeedElemRestrictionDestroy_Cuda()
395 CeedCallBackend(CeedFree(&impl->h_offsets_owned)); in CeedElemRestrictionDestroy_Cuda()
396 CeedCallCuda(ceed, cudaFree((CeedInt *)impl->d_offsets_owned)); in CeedElemRestrictionDestroy_Cuda()
397 CeedCallCuda(ceed, cudaFree((CeedInt *)impl->d_t_offsets)); in CeedElemRestrictionDestroy_Cuda()
398 CeedCallCuda(ceed, cudaFree((CeedInt *)impl->d_t_indices)); in CeedElemRestrictionDestroy_Cuda()
399 CeedCallCuda(ceed, cudaFree((CeedInt *)impl->d_l_vec_indices)); in CeedElemRestrictionDestroy_Cuda()
400 CeedCallBackend(CeedFree(&impl->h_orients_owned)); in CeedElemRestrictionDestroy_Cuda()
401 CeedCallCuda(ceed, cudaFree((bool *)impl->d_orients_owned)); in CeedElemRestrictionDestroy_Cuda()
402 CeedCallBackend(CeedFree(&impl->h_curl_orients_owned)); in CeedElemRestrictionDestroy_Cuda()
403 CeedCallCuda(ceed, cudaFree((CeedInt8 *)impl->d_curl_orients_owned)); in CeedElemRestrictionDestroy_Cuda()
404 CeedCallBackend(CeedFree(&impl->h_offsets_at_points_owned)); in CeedElemRestrictionDestroy_Cuda()
405 CeedCallCuda(ceed, cudaFree((CeedInt *)impl->d_offsets_at_points_owned)); in CeedElemRestrictionDestroy_Cuda()
406 CeedCallBackend(CeedFree(&impl->h_points_per_elem_owned)); in CeedElemRestrictionDestroy_Cuda()
407 CeedCallCuda(ceed, cudaFree((CeedInt *)impl->d_points_per_elem_owned)); in CeedElemRestrictionDestroy_Cuda()
408 CeedCallBackend(CeedFree(&impl)); in CeedElemRestrictionDestroy_Cuda()
423 CeedElemRestriction_Cuda *impl; in CeedElemRestrictionOffset_Cuda() local
426 CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl)); in CeedElemRestrictionOffset_Cuda()
438 impl->num_nodes = num_nodes; in CeedElemRestrictionOffset_Cuda()
477 CeedCallCuda(ceed, cudaMalloc((void **)&impl->d_l_vec_indices, num_nodes * sizeof(CeedInt))); in CeedElemRestrictionOffset_Cuda()
478 …CeedCallCuda(ceed, cudaMemcpy((CeedInt *)impl->d_l_vec_indices, l_vec_indices, num_nodes * sizeof(… in CeedElemRestrictionOffset_Cuda()
480 CeedCallCuda(ceed, cudaMalloc((void **)&impl->d_t_offsets, size_offsets * sizeof(CeedInt))); in CeedElemRestrictionOffset_Cuda()
481 …CeedCallCuda(ceed, cudaMemcpy((CeedInt *)impl->d_t_offsets, t_offsets, size_offsets * sizeof(CeedI… in CeedElemRestrictionOffset_Cuda()
483 CeedCallCuda(ceed, cudaMalloc((void **)&impl->d_t_indices, size_indices * sizeof(CeedInt))); in CeedElemRestrictionOffset_Cuda()
484 …CeedCallCuda(ceed, cudaMemcpy((CeedInt *)impl->d_t_indices, t_indices, size_indices * sizeof(CeedI… in CeedElemRestrictionOffset_Cuda()
504 CeedElemRestriction_Cuda *impl; in CeedElemRestrictionCreate_Cuda() local
525 CeedCallBackend(CeedCalloc(1, &impl)); in CeedElemRestrictionCreate_Cuda()
526 impl->num_nodes = size; in CeedElemRestrictionCreate_Cuda()
527 CeedCallBackend(CeedElemRestrictionSetData(rstr, impl)); in CeedElemRestrictionCreate_Cuda()
567 …SetHostCeedIntArray(offsets, copy_mode, at_points_size, &impl->h_offsets_at_points_owned, &impl->h… in CeedElemRestrictionCreate_Cuda()
568 &impl->h_offsets_at_points)); in CeedElemRestrictionCreate_Cuda()
569 …CeedCallCuda(ceed, cudaMalloc((void **)&impl->d_offsets_at_points_owned, at_points_size * sizeof(C… in CeedElemRestrictionCreate_Cuda()
570 …CeedCallCuda(ceed, cudaMemcpy((CeedInt **)impl->d_offsets_at_points_owned, impl->h_offsets_at_poin… in CeedElemRestrictionCreate_Cuda()
572 impl->d_offsets_at_points = (CeedInt *)impl->d_offsets_at_points_owned; in CeedElemRestrictionCreate_Cuda()
580 …CeedCallBackend(CeedSetHostCeedIntArray(points_per_elem, CEED_OWN_POINTER, num_elem, &impl->h_poin… in CeedElemRestrictionCreate_Cuda()
581 … &impl->h_points_per_elem_borrowed, &impl->h_points_per_elem)); in CeedElemRestrictionCreate_Cuda()
582 …CeedCallCuda(ceed, cudaMalloc((void **)&impl->d_points_per_elem_owned, num_elem * sizeof(CeedInt))… in CeedElemRestrictionCreate_Cuda()
584 …cudaMemcpy((CeedInt **)impl->d_points_per_elem_owned, impl->h_points_per_elem, num_elem * sizeof(C… in CeedElemRestrictionCreate_Cuda()
585 impl->d_points_per_elem = (CeedInt *)impl->d_points_per_elem_owned; in CeedElemRestrictionCreate_Cuda()
592 …edSetHostCeedIntArray(offsets, copy_mode, size, &impl->h_offsets_owned, &impl->h_offsets_borrowed,… in CeedElemRestrictionCreate_Cuda()
593 CeedCallCuda(ceed, cudaMalloc((void **)&impl->d_offsets_owned, size * sizeof(CeedInt))); in CeedElemRestrictionCreate_Cuda()
594 …CeedCallCuda(ceed, cudaMemcpy((CeedInt *)impl->d_offsets_owned, impl->h_offsets, size * sizeof(Cee… in CeedElemRestrictionCreate_Cuda()
595 impl->d_offsets = (CeedInt *)impl->d_offsets_owned; in CeedElemRestrictionCreate_Cuda()
599 …edSetDeviceCeedIntArray_Cuda(ceed, offsets, copy_mode, size, &impl->d_offsets_owned, &impl->d_offs… in CeedElemRestrictionCreate_Cuda()
600 (const CeedInt **)&impl->d_offsets)); in CeedElemRestrictionCreate_Cuda()
601 CeedCallBackend(CeedMalloc(size, &impl->h_offsets_owned)); in CeedElemRestrictionCreate_Cuda()
602 …CeedCallCuda(ceed, cudaMemcpy((CeedInt *)impl->h_offsets_owned, impl->d_offsets, size * sizeof(Cee… in CeedElemRestrictionCreate_Cuda()
603 impl->h_offsets = impl->h_offsets_owned; in CeedElemRestrictionCreate_Cuda()
612 …(CeedSetHostBoolArray(orients, copy_mode, size, &impl->h_orients_owned, &impl->h_orients_borrowed,… in CeedElemRestrictionCreate_Cuda()
613 CeedCallCuda(ceed, cudaMalloc((void **)&impl->d_orients_owned, size * sizeof(bool))); in CeedElemRestrictionCreate_Cuda()
614 …CeedCallCuda(ceed, cudaMemcpy((bool *)impl->d_orients_owned, impl->h_orients, size * sizeof(bool),… in CeedElemRestrictionCreate_Cuda()
615 impl->d_orients = impl->d_orients_owned; in CeedElemRestrictionCreate_Cuda()
618 …(CeedSetDeviceBoolArray_Cuda(ceed, orients, copy_mode, size, &impl->d_orients_owned, &impl->d_orie… in CeedElemRestrictionCreate_Cuda()
619 (const bool **)&impl->d_orients)); in CeedElemRestrictionCreate_Cuda()
620 CeedCallBackend(CeedMalloc(size, &impl->h_orients_owned)); in CeedElemRestrictionCreate_Cuda()
621 …CeedCallCuda(ceed, cudaMemcpy((bool *)impl->h_orients_owned, impl->d_orients, size * sizeof(bool),… in CeedElemRestrictionCreate_Cuda()
622 impl->h_orients = impl->h_orients_owned; in CeedElemRestrictionCreate_Cuda()
628 …eedSetHostCeedInt8Array(curl_orients, copy_mode, 3 * size, &impl->h_curl_orients_owned, &impl->h_c… in CeedElemRestrictionCreate_Cuda()
629 &impl->h_curl_orients)); in CeedElemRestrictionCreate_Cuda()
630 … CeedCallCuda(ceed, cudaMalloc((void **)&impl->d_curl_orients_owned, 3 * size * sizeof(CeedInt8))); in CeedElemRestrictionCreate_Cuda()
632 …cudaMemcpy((CeedInt8 *)impl->d_curl_orients_owned, impl->h_curl_orients, 3 * size * sizeof(CeedInt… in CeedElemRestrictionCreate_Cuda()
633 impl->d_curl_orients = impl->d_curl_orients_owned; in CeedElemRestrictionCreate_Cuda()
636 …CeedSetDeviceCeedInt8Array_Cuda(ceed, curl_orients, copy_mode, 3 * size, &impl->d_curl_orients_own… in CeedElemRestrictionCreate_Cuda()
637 … &impl->d_curl_orients_borrowed, (const CeedInt8 **)&impl->d_curl_orients)); in CeedElemRestrictionCreate_Cuda()
638 CeedCallBackend(CeedMalloc(3 * size, &impl->h_curl_orients_owned)); in CeedElemRestrictionCreate_Cuda()
640 …cudaMemcpy((CeedInt8 *)impl->h_curl_orients_owned, impl->d_curl_orients, 3 * size * sizeof(CeedInt… in CeedElemRestrictionCreate_Cuda()
641 impl->h_curl_orients = impl->h_curl_orients_owned; in CeedElemRestrictionCreate_Cuda()