28   CeedElemRestriction_Hip *impl;  in CeedElemRestrictionSetupCompile_Hip()  local
30   CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl));  in CeedElemRestrictionSetupCompile_Hip()
41   is_deterministic = impl->d_l_vec_indices != NULL;  in CeedElemRestrictionSetupCompile_Hip()
54 …CeedCallBackend(CeedCompile_Hip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE…  in CeedElemRestrictionSetupCompile_Hip()
57 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "StridedNoTranspose", &impl->ApplyNoTranspos…  in CeedElemRestrictionSetupCompile_Hip()
58 … CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "StridedTranspose", &impl->ApplyTranspose));  in CeedElemRestrictionSetupCompile_Hip()
63 …CeedCallBackend(CeedCompile_Hip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE…  in CeedElemRestrictionSetupCompile_Hip()
64 …     "RSTR_NUM_COMP", num_comp, "RSTR_NUM_NODES", impl->num_nodes, "RSTR_COMP_STRIDE", comp_stride,  in CeedElemRestrictionSetupCompile_Hip()
66 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OffsetNoTranspose", &impl->ApplyNoTranspose…  in CeedElemRestrictionSetupCompile_Hip()
67 …  CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OffsetTranspose", &impl->ApplyTranspose));  in CeedElemRestrictionSetupCompile_Hip()
74 …CeedCallBackend(CeedCompile_Hip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE…  in CeedElemRestrictionSetupCompile_Hip()
75 …     "RSTR_NUM_COMP", num_comp, "RSTR_NUM_NODES", impl->num_nodes, "RSTR_COMP_STRIDE", comp_stride,  in CeedElemRestrictionSetupCompile_Hip()
77 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OffsetNoTranspose", &impl->ApplyNoTranspose…  in CeedElemRestrictionSetupCompile_Hip()
78 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "AtPointsTranspose", &impl->ApplyTranspose));  in CeedElemRestrictionSetupCompile_Hip()
85 …CeedCallBackend(CeedCompile_Hip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE…  in CeedElemRestrictionSetupCompile_Hip()
86 …     "RSTR_NUM_COMP", num_comp, "RSTR_NUM_NODES", impl->num_nodes, "RSTR_COMP_STRIDE", comp_stride,  in CeedElemRestrictionSetupCompile_Hip()
88 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OrientedNoTranspose", &impl->ApplyNoTranspo…  in CeedElemRestrictionSetupCompile_Hip()
89 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OffsetNoTranspose", &impl->ApplyUnsignedNoT…  in CeedElemRestrictionSetupCompile_Hip()
90 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OrientedTranspose", &impl->ApplyTranspose));  in CeedElemRestrictionSetupCompile_Hip()
91 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OffsetTranspose", &impl->ApplyUnsignedTrans…  in CeedElemRestrictionSetupCompile_Hip()
98 …CeedCallBackend(CeedCompile_Hip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE…  in CeedElemRestrictionSetupCompile_Hip()
99 …     "RSTR_NUM_COMP", num_comp, "RSTR_NUM_NODES", impl->num_nodes, "RSTR_COMP_STRIDE", comp_stride,  in CeedElemRestrictionSetupCompile_Hip()
101 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "CurlOrientedNoTranspose", &impl->ApplyNoTra…  in CeedElemRestrictionSetupCompile_Hip()
102 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "CurlOrientedUnsignedNoTranspose", &impl->Ap…  in CeedElemRestrictionSetupCompile_Hip()
103 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OffsetNoTranspose", &impl->ApplyUnorientedN…  in CeedElemRestrictionSetupCompile_Hip()
104 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "CurlOrientedTranspose", &impl->ApplyTranspo…  in CeedElemRestrictionSetupCompile_Hip()
105 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "CurlOrientedUnsignedTranspose", &impl->Appl…  in CeedElemRestrictionSetupCompile_Hip()
106 …CeedCallBackend(CeedGetKernel_Hip(ceed, impl->module, "OffsetTranspose", &impl->ApplyUnorientedTra…  in CeedElemRestrictionSetupCompile_Hip()
123   CeedElemRestriction_Hip *impl;  in CeedElemRestrictionApply_Hip_Core()  local
125   CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl));  in CeedElemRestrictionApply_Hip_Core()
130   if (!impl->module) {  in CeedElemRestrictionApply_Hip_Core()
151     const CeedInt grid       = CeedDivUpInt(impl->num_nodes, block_size);  in CeedElemRestrictionApply_Hip_Core()
157         CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyNoTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
161         void *args[] = {&impl->d_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
163         CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyNoTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
167           void *args[] = {&impl->d_offsets, &impl->d_orients, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
169           CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyNoTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
171           void *args[] = {&impl->d_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
173 …  CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnsignedNoTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
178           void *args[] = {&impl->d_offsets, &impl->d_curl_orients, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
180           CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyNoTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
182           void *args[] = {&impl->d_offsets, &impl->d_curl_orients, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
184 …  CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnsignedNoTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
186           void *args[] = {&impl->d_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
188 …CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnorientedNoTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
194     const bool    is_deterministic = impl->d_l_vec_indices != NULL;  in CeedElemRestrictionApply_Hip_Core()
196     const CeedInt grid             = CeedDivUpInt(impl->num_nodes, block_size);  in CeedElemRestrictionApply_Hip_Core()
202         CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
206           void *args[] = {&impl->d_offsets, &impl->d_points_per_elem, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
208           CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
210 …void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_points_per_elem, &impl->d_t_o…  in CeedElemRestrictionApply_Hip_Core()
212           CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
217           void *args[] = {&impl->d_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
219           CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
221 …       void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
223           CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
229             void *args[] = {&impl->d_offsets, &impl->d_orients, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
231             CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
233 …void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &impl->d_orients, …  in CeedElemRestrictionApply_Hip_Core()
235             CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
239             void *args[] = {&impl->d_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
241 …    CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnsignedTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
243 …       void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
245 …    CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnsignedTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
252             void *args[] = {&impl->d_offsets, &impl->d_curl_orients, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
254             CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
256 …void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &impl->d_curl_orie…  in CeedElemRestrictionApply_Hip_Core()
258             CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
262             void *args[] = {&impl->d_offsets, &impl->d_curl_orients, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
264 …    CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnsignedTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
266 …void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &impl->d_curl_orie…  in CeedElemRestrictionApply_Hip_Core()
268 …    CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnsignedTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
272             void *args[] = {&impl->d_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
274 …  CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnorientedTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
276 …       void *args[] = {&impl->d_l_vec_indices, &impl->d_t_indices, &impl->d_t_offsets, &d_u, &d_v};  in CeedElemRestrictionApply_Hip_Core()
278 …  CeedCallBackend(CeedRunKernel_Hip(ceed, impl->ApplyUnorientedTranspose, grid, block_size, args));  in CeedElemRestrictionApply_Hip_Core()
321   CeedElemRestriction_Hip *impl;  in CeedElemRestrictionGetOffsets_Hip()  local
324   CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl));  in CeedElemRestrictionGetOffsets_Hip()
328       *offsets = rstr_type == CEED_RESTRICTION_POINTS ? impl->h_offsets_at_points : impl->h_offsets;  in CeedElemRestrictionGetOffsets_Hip()
331       *offsets = rstr_type == CEED_RESTRICTION_POINTS ? impl->d_offsets_at_points : impl->d_offsets;  in CeedElemRestrictionGetOffsets_Hip()
341   CeedElemRestriction_Hip *impl;  in CeedElemRestrictionGetOrientations_Hip()  local
342   CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl));  in CeedElemRestrictionGetOrientations_Hip()
346       *orients = impl->h_orients;  in CeedElemRestrictionGetOrientations_Hip()
349       *orients = impl->d_orients;  in CeedElemRestrictionGetOrientations_Hip()
359   CeedElemRestriction_Hip *impl;  in CeedElemRestrictionGetCurlOrientations_Hip()  local
360   CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl));  in CeedElemRestrictionGetCurlOrientations_Hip()
364       *curl_orients = impl->h_curl_orients;  in CeedElemRestrictionGetCurlOrientations_Hip()
367       *curl_orients = impl->d_curl_orients;  in CeedElemRestrictionGetCurlOrientations_Hip()
389   CeedElemRestriction_Hip *impl;  in CeedElemRestrictionDestroy_Hip()  local
391   CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl));  in CeedElemRestrictionDestroy_Hip()
393   if (impl->module) {  in CeedElemRestrictionDestroy_Hip()
394     CeedCallHip(ceed, hipModuleUnload(impl->module));  in CeedElemRestrictionDestroy_Hip()
396   CeedCallBackend(CeedFree(&impl->h_offsets_owned));  in CeedElemRestrictionDestroy_Hip()
397   CeedCallHip(ceed, hipFree((CeedInt *)impl->d_offsets_owned));  in CeedElemRestrictionDestroy_Hip()
398   CeedCallHip(ceed, hipFree((CeedInt *)impl->d_t_offsets));  in CeedElemRestrictionDestroy_Hip()
399   CeedCallHip(ceed, hipFree((CeedInt *)impl->d_t_indices));  in CeedElemRestrictionDestroy_Hip()
400   CeedCallHip(ceed, hipFree((CeedInt *)impl->d_l_vec_indices));  in CeedElemRestrictionDestroy_Hip()
401   CeedCallBackend(CeedFree(&impl->h_orients_owned));  in CeedElemRestrictionDestroy_Hip()
402   CeedCallHip(ceed, hipFree((bool *)impl->d_orients_owned));  in CeedElemRestrictionDestroy_Hip()
403   CeedCallBackend(CeedFree(&impl->h_curl_orients_owned));  in CeedElemRestrictionDestroy_Hip()
404   CeedCallHip(ceed, hipFree((CeedInt8 *)impl->d_curl_orients_owned));  in CeedElemRestrictionDestroy_Hip()
405   CeedCallBackend(CeedFree(&impl->h_offsets_at_points_owned));  in CeedElemRestrictionDestroy_Hip()
406   CeedCallHip(ceed, hipFree((CeedInt8 *)impl->d_offsets_at_points_owned));  in CeedElemRestrictionDestroy_Hip()
407   CeedCallBackend(CeedFree(&impl->h_points_per_elem_owned));  in CeedElemRestrictionDestroy_Hip()
408   CeedCallHip(ceed, hipFree((CeedInt *)impl->d_points_per_elem_owned));  in CeedElemRestrictionDestroy_Hip()
409   CeedCallBackend(CeedFree(&impl));  in CeedElemRestrictionDestroy_Hip()
424   CeedElemRestriction_Hip *impl;  in CeedElemRestrictionOffset_Hip()  local
427   CeedCallBackend(CeedElemRestrictionGetData(rstr, &impl));  in CeedElemRestrictionOffset_Hip()
439   impl->num_nodes = num_nodes;  in CeedElemRestrictionOffset_Hip()
478   CeedCallHip(ceed, hipMalloc((void **)&impl->d_l_vec_indices, num_nodes * sizeof(CeedInt)));  in CeedElemRestrictionOffset_Hip()
479 …CeedCallHip(ceed, hipMemcpy((CeedInt *)impl->d_l_vec_indices, l_vec_indices, num_nodes * sizeof(Ce…  in CeedElemRestrictionOffset_Hip()
481   CeedCallHip(ceed, hipMalloc((void **)&impl->d_t_offsets, size_offsets * sizeof(CeedInt)));  in CeedElemRestrictionOffset_Hip()
482 …CeedCallHip(ceed, hipMemcpy((CeedInt *)impl->d_t_offsets, t_offsets, size_offsets * sizeof(CeedInt…  in CeedElemRestrictionOffset_Hip()
484   CeedCallHip(ceed, hipMalloc((void **)&impl->d_t_indices, size_indices * sizeof(CeedInt)));  in CeedElemRestrictionOffset_Hip()
485 …CeedCallHip(ceed, hipMemcpy((CeedInt *)impl->d_t_indices, t_indices, size_indices * sizeof(CeedInt…  in CeedElemRestrictionOffset_Hip()
505   CeedElemRestriction_Hip *impl;  in CeedElemRestrictionCreate_Hip()  local
526   CeedCallBackend(CeedCalloc(1, &impl));  in CeedElemRestrictionCreate_Hip()
527   impl->num_nodes = size;  in CeedElemRestrictionCreate_Hip()
528   CeedCallBackend(CeedElemRestrictionSetData(rstr, impl));  in CeedElemRestrictionCreate_Hip()
568 …SetHostCeedIntArray(offsets, copy_mode, at_points_size, &impl->h_offsets_at_points_owned, &impl->h…  in CeedElemRestrictionCreate_Hip()
569                                             &impl->h_offsets_at_points));  in CeedElemRestrictionCreate_Hip()
570 …CeedCallHip(ceed, hipMalloc((void **)&impl->d_offsets_at_points_owned, at_points_size * sizeof(Cee…  in CeedElemRestrictionCreate_Hip()
571 …CeedCallHip(ceed, hipMemcpy((CeedInt **)impl->d_offsets_at_points_owned, impl->h_offsets_at_points…  in CeedElemRestrictionCreate_Hip()
573     impl->d_offsets_at_points = (CeedInt *)impl->d_offsets_at_points_owned;  in CeedElemRestrictionCreate_Hip()
581 …CeedCallBackend(CeedSetHostCeedIntArray(points_per_elem, CEED_OWN_POINTER, num_elem, &impl->h_poin…  in CeedElemRestrictionCreate_Hip()
582 …                                     &impl->h_points_per_elem_borrowed, &impl->h_points_per_elem));  in CeedElemRestrictionCreate_Hip()
583 … CeedCallHip(ceed, hipMalloc((void **)&impl->d_points_per_elem_owned, num_elem * sizeof(CeedInt)));  in CeedElemRestrictionCreate_Hip()
585 …hipMemcpy((CeedInt **)impl->d_points_per_elem_owned, impl->h_points_per_elem, num_elem * sizeof(Ce…  in CeedElemRestrictionCreate_Hip()
586     impl->d_points_per_elem = (CeedInt *)impl->d_points_per_elem_owned;  in CeedElemRestrictionCreate_Hip()
593 …edSetHostCeedIntArray(offsets, copy_mode, size, &impl->h_offsets_owned, &impl->h_offsets_borrowed,…  in CeedElemRestrictionCreate_Hip()
594         CeedCallHip(ceed, hipMalloc((void **)&impl->d_offsets_owned, size * sizeof(CeedInt)));  in CeedElemRestrictionCreate_Hip()
595 …CeedCallHip(ceed, hipMemcpy((CeedInt **)impl->d_offsets_owned, impl->h_offsets, size * sizeof(Ceed…  in CeedElemRestrictionCreate_Hip()
596         impl->d_offsets = (CeedInt *)impl->d_offsets_owned;  in CeedElemRestrictionCreate_Hip()
600 …eedSetDeviceCeedIntArray_Hip(ceed, offsets, copy_mode, size, &impl->d_offsets_owned, &impl->d_offs…  in CeedElemRestrictionCreate_Hip()
601                                                       (const CeedInt **)&impl->d_offsets));  in CeedElemRestrictionCreate_Hip()
602         CeedCallBackend(CeedMalloc(size, &impl->h_offsets_owned));  in CeedElemRestrictionCreate_Hip()
603 …CeedCallHip(ceed, hipMemcpy((CeedInt **)impl->h_offsets_owned, impl->d_offsets, size * sizeof(Ceed…  in CeedElemRestrictionCreate_Hip()
604         impl->h_offsets = impl->h_offsets_owned;  in CeedElemRestrictionCreate_Hip()
613 …(CeedSetHostBoolArray(orients, copy_mode, size, &impl->h_orients_owned, &impl->h_orients_borrowed,…  in CeedElemRestrictionCreate_Hip()
614           CeedCallHip(ceed, hipMalloc((void **)&impl->d_orients_owned, size * sizeof(bool)));  in CeedElemRestrictionCreate_Hip()
615 …CeedCallHip(ceed, hipMemcpy((bool *)impl->d_orients_owned, impl->h_orients, size * sizeof(bool), h…  in CeedElemRestrictionCreate_Hip()
616           impl->d_orients = impl->d_orients_owned;  in CeedElemRestrictionCreate_Hip()
619 …d(CeedSetDeviceBoolArray_Hip(ceed, orients, copy_mode, size, &impl->d_orients_owned, &impl->d_orie…  in CeedElemRestrictionCreate_Hip()
620                                                      (const bool **)&impl->d_orients));  in CeedElemRestrictionCreate_Hip()
621           CeedCallBackend(CeedMalloc(size, &impl->h_orients_owned));  in CeedElemRestrictionCreate_Hip()
622 …CeedCallHip(ceed, hipMemcpy((bool *)impl->h_orients_owned, impl->d_orients, size * sizeof(bool), h…  in CeedElemRestrictionCreate_Hip()
623           impl->h_orients = impl->h_orients_owned;  in CeedElemRestrictionCreate_Hip()
629 …eedSetHostCeedInt8Array(curl_orients, copy_mode, 3 * size, &impl->h_curl_orients_owned, &impl->h_c…  in CeedElemRestrictionCreate_Hip()
630                                                    &impl->h_curl_orients));  in CeedElemRestrictionCreate_Hip()
631 …   CeedCallHip(ceed, hipMalloc((void **)&impl->d_curl_orients_owned, 3 * size * sizeof(CeedInt8)));  in CeedElemRestrictionCreate_Hip()
633 …hipMemcpy((CeedInt8 *)impl->d_curl_orients_owned, impl->h_curl_orients, 3 * size * sizeof(CeedInt8…  in CeedElemRestrictionCreate_Hip()
634           impl->d_curl_orients = impl->d_curl_orients_owned;  in CeedElemRestrictionCreate_Hip()
637 …(CeedSetDeviceCeedInt8Array_Hip(ceed, curl_orients, copy_mode, 3 * size, &impl->d_curl_orients_own…  in CeedElemRestrictionCreate_Hip()
638 …                        &impl->d_curl_orients_borrowed, (const CeedInt8 **)&impl->d_curl_orients));  in CeedElemRestrictionCreate_Hip()
639           CeedCallBackend(CeedMalloc(3 * size, &impl->h_curl_orients_owned));  in CeedElemRestrictionCreate_Hip()
641 …hipMemcpy((CeedInt8 *)impl->h_curl_orients_owned, impl->d_curl_orients, 3 * size * sizeof(CeedInt8…  in CeedElemRestrictionCreate_Hip()
642           impl->h_curl_orients = impl->h_curl_orients_owned;  in CeedElemRestrictionCreate_Hip()