| /libCEED/backends/memcheck/ |
| H A D | ceed-memcheck-restriction.c | 20 CeedInt elem_size, num_comp, num_elem; in CeedElemRestrictionGetBackendStrides_Memcheck() local
22 CeedCallBackend(CeedElemRestrictionGetElementSize(rstr, &elem_size)); in CeedElemRestrictionGetBackendStrides_Memcheck()
28 strides[2] = num_comp * elem_size; in CeedElemRestrictionGetBackendStrides_Memcheck()
47 … CeedInt start, CeedInt stop, CeedInt num_elem, CeedInt elem_size, in CeedElemRestrictionApplyStridedNoTranspose_Memcheck_Core() argument
61 for (CeedSize n = 0; n < elem_size; n++) { in CeedElemRestrictionApplyStridedNoTranspose_Memcheck_Core()
63 vv[e * elem_size * num_comp + (k * elem_size + n) * block_size + j - v_offset] = in CeedElemRestrictionApplyStridedNoTranspose_Memcheck_Core()
74 … CeedInt elem_size, CeedSize v_offset, const CeedScalar *__restrict__ uu, in CeedElemRestrictionApplyOffsetNoTranspose_Memcheck_Core() argument
82 CeedPragmaSIMD for (CeedSize i = 0; i < elem_size * block_size; i++) { in CeedElemRestrictionApplyOffsetNoTranspose_Memcheck_Core()
83 …vv[elem_size * (k * block_size + e * num_comp) + i - v_offset] = uu[impl->offsets[i + e * elem_siz… in CeedElemRestrictionApplyOffsetNoTranspose_Memcheck_Core()
92 … CeedInt stop, CeedInt num_elem, CeedInt elem_size, CeedSize v_offset, in CeedElemRestrictionApplyOrientedNoTranspose_Memcheck_Core() argument
[all …]
|
| /libCEED/backends/ref/ |
| H A D | ceed-ref-restriction.c | 21 … const CeedInt elem_size, CeedSize v_offset, const CeedScalar *__restrict__ uu, in CeedElemRestrictionApplyStridedNoTranspose_Ref_Core() argument
32 for (CeedSize n = 0; n < elem_size; n++) { in CeedElemRestrictionApplyStridedNoTranspose_Ref_Core()
34 vv[e * elem_size * num_comp + (k * elem_size + n) * block_size + j - v_offset] = in CeedElemRestrictionApplyStridedNoTranspose_Ref_Core()
35 … uu[n + k * elem_size + CeedIntMin(e + j, num_elem - 1) * elem_size * (CeedSize)num_comp]; in CeedElemRestrictionApplyStridedNoTranspose_Ref_Core()
47 for (CeedSize n = 0; n < elem_size; n++) { in CeedElemRestrictionApplyStridedNoTranspose_Ref_Core()
49 vv[e * elem_size * num_comp + (k * elem_size + n) * block_size + j - v_offset] = in CeedElemRestrictionApplyStridedNoTranspose_Ref_Core()
61 … const CeedInt num_elem, const CeedInt elem_size, const CeedSize v_offset, in CeedElemRestrictionApplyOffsetNoTranspose_Ref_Core() argument
69 CeedPragmaSIMD for (CeedSize i = 0; i < elem_size * block_size; i++) { in CeedElemRestrictionApplyOffsetNoTranspose_Ref_Core()
70 …vv[elem_size * (k * block_size + e * num_comp) + i - v_offset] = uu[impl->offsets[i + e * elem_siz… in CeedElemRestrictionApplyOffsetNoTranspose_Ref_Core()
79 … const CeedInt num_elem, const CeedInt elem_size, const CeedSize v_offset, in CeedElemRestrictionApplyOrientedNoTranspose_Ref_Core() argument
[all …]
|
| H A D | ceed-ref-operator.c | 258 CeedInt elem_size, size, num_comp; in CeedOperatorInputBasis_Ref() local
275 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorInputBasis_Ref()
290 …vecs_in[i], CEED_MEM_HOST, CEED_USE_POINTER, &e_data_full[i][(CeedSize)e * elem_size * num_comp])); in CeedOperatorInputBasis_Ref()
308 CeedInt elem_size, num_comp; in CeedOperatorOutputBasis_Ref() local
315 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorOutputBasis_Ref()
329 … &e_data_full[i + num_input_fields][(CeedSize)e * elem_size * num_comp])); in CeedOperatorOutputBasis_Ref()
893 CeedInt elem_size, size, num_comp; in CeedOperatorInputBasisAtPoints_Ref() local
936 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorInputBasisAtPoints_Ref()
937 …l->e_vecs_in[i], CEED_MEM_HOST, CEED_USE_POINTER, &e_data[i][(CeedSize)e * elem_size * num_comp])); in CeedOperatorInputBasisAtPoints_Ref()
1452 CeedInt elem_size = 0; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Ref() local
[all …]
|
| /libCEED/backends/sycl-ref/ |
| H A D | ceed-sycl-restriction.sycl.cpp | 29 const CeedInt elem_size = impl->elem_size; in CeedElemRestrictionStridedNoTranspose_Sycl() local
35 sycl::range<1> kernel_range(num_elem * elem_size); in CeedElemRestrictionStridedNoTranspose_Sycl()
41 const CeedInt loc_node = node % elem_size; in CeedElemRestrictionStridedNoTranspose_Sycl()
42 const CeedInt elem = node / elem_size; in CeedElemRestrictionStridedNoTranspose_Sycl()
45 …v[loc_node + comp * elem_size * num_elem + elem * elem_size] = u[loc_node * stride_nodes + comp * … in CeedElemRestrictionStridedNoTranspose_Sycl()
56 const CeedInt elem_size = impl->elem_size; in CeedElemRestrictionOffsetNoTranspose_Sycl() local
62 sycl::range<1> kernel_range(num_elem * elem_size); in CeedElemRestrictionOffsetNoTranspose_Sycl()
69 const CeedInt loc_node = node % elem_size; in CeedElemRestrictionOffsetNoTranspose_Sycl()
70 const CeedInt elem = node / elem_size; in CeedElemRestrictionOffsetNoTranspose_Sycl()
73 v[loc_node + comp * elem_size * num_elem + elem * elem_size] = u[ind + comp * comp_stride]; in CeedElemRestrictionOffsetNoTranspose_Sycl()
[all …]
|
| H A D | ceed-sycl-ref-operator.sycl.cpp | 375 CeedInt Q, num_elem, elem_size, num_input_fields, num_output_fields, size; in CeedOperatorApplyAdd_Sycl() local
418 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorApplyAdd_Sycl()
1003 … num_B_out_mats_to_load = 0, size_B_out = 0, num_qpts = 0, elem_size = 0, num_elem, num_comp, in CeedOperatorAssembleSingleSetup_Sycl() local
1039 CeedCallBackend(CeedElemRestrictionGetElementSize(rstr_in, &elem_size)); in CeedOperatorAssembleSingleSetup_Sycl()
1053 size_B_in += dim * elem_size * num_qpts; in CeedOperatorAssembleSingleSetup_Sycl()
1056 size_B_in += elem_size * num_qpts; in CeedOperatorAssembleSingleSetup_Sycl()
1089 size_B_out += dim * elem_size * num_qpts; in CeedOperatorAssembleSingleSetup_Sycl()
1092 size_B_out += elem_size * num_qpts; in CeedOperatorAssembleSingleSetup_Sycl()
1113 asmb->block_size_x = elem_size; in CeedOperatorAssembleSingleSetup_Sycl()
1114 asmb->block_size_y = elem_size; in CeedOperatorAssembleSingleSetup_Sycl()
[all …]
|
| /libCEED/interface/ |
| H A D | ceed-elemrestriction.c | 39 CeedInt elem_size) { in CeedPermutePadOffsets() argument
42 for (CeedInt k = 0; k < elem_size; k++) { in CeedPermutePadOffsets()
43 …block_offsets[e * elem_size + k * block_size + j] = offsets[CeedIntMin(e + j, num_elem - 1) * elem… in CeedPermutePadOffsets()
64 … bool *block_orients, CeedInt num_block, CeedInt num_elem, CeedInt block_size, CeedInt elem_size) { in CeedPermutePadOrients() argument
67 for (CeedInt k = 0; k < elem_size; k++) { in CeedPermutePadOrients()
68 …block_orients[e * elem_size + k * block_size + j] = orients[CeedIntMin(e + j, num_elem - 1) * elem… in CeedPermutePadOrients()
90 CeedInt elem_size) { in CeedPermutePadCurlOrients() argument
93 for (CeedInt k = 0; k < elem_size; k++) { in CeedPermutePadCurlOrients()
94 …block_curl_orients[e * elem_size + k * block_size + j] = curl_orients[CeedIntMin(e + j, num_elem -… in CeedPermutePadCurlOrients()
657 int CeedElemRestrictionCreate(Ceed ceed, CeedInt num_elem, CeedInt elem_size, CeedInt num_comp, Cee… in CeedElemRestrictionCreate() argument
[all …]
|
| /libCEED/tests/ |
| H A D | t217-elemrestriction.c | 10 CeedInt num_elem = 6, elem_size = 2; in main() local
11 CeedInt ind[elem_size * num_elem]; in main()
12 bool orients[elem_size * num_elem]; in main()
21 CeedVectorCreate(ceed, num_elem * elem_size, &y); in main()
29 …CeedElemRestrictionCreateOriented(ceed, num_elem, elem_size, 1, 1, num_elem + 1, CEED_MEM_HOST, CE… in main()
38 for (CeedInt j = 0; j < elem_size; j++) { in main()
39 CeedInt k = j + elem_size * i; in main()
|
| H A D | t213-elemrestriction.c | 14 CeedInt elem_size = 2; in main() local
18 CeedInt ind[elem_size * num_elem]; in main()
19 CeedInt *ceed_ind = malloc(sizeof(CeedInt) * elem_size * num_elem); in main()
33 CeedVectorCreate(ceed, num_comp * num_blk * blk_size * elem_size, &y); in main()
39 memcpy(ceed_ind, ind, sizeof(CeedInt) * elem_size * num_elem); in main()
40 …CeedElemRestrictionCreateBlocked(ceed, num_elem, elem_size, blk_size, num_comp, num_elem + 1, num_… in main()
50 for (CeedInt i = 0; i < elem_size; i++) { // Node in main()
56 if (y_array[index] != x_array[ind[k * elem_size + i] + j * (num_elem + 1)]) in main()
|
| H A D | t208-elemrestriction.c | 12 CeedInt elem_size = 2; in main() local
14 CeedInt ind[elem_size * num_elem]; in main()
24 CeedVectorCreate(ceed, blk_size * elem_size, &y); in main()
30 …CeedElemRestrictionCreateBlocked(ceed, num_elem, elem_size, blk_size, 1, 1, num_elem + 1, CEED_MEM… in main()
39 for (CeedInt i = 0; i < elem_size; i++) { // Node in main()
44 …* e_layout[0] + j * e_layout[1] * blk_size + block * e_layout[2] * blk_size - blk_size * elem_size; in main()
45 if (y_array[index] != x_array[ind[k * elem_size + i]]) { in main()
|
| H A D | t202-elemrestriction.c | 12 CeedInt elem_size = 2; in main() local
15 CeedInt ind[elem_size * num_elem]; in main()
25 CeedVectorCreate(ceed, num_blk * blk_size * elem_size, &y); in main()
31 …CeedElemRestrictionCreateBlocked(ceed, num_elem, elem_size, blk_size, 1, 1, num_elem + 1, CEED_MEM… in main()
40 for (CeedInt i = 0; i < elem_size; i++) { // Node in main()
46 if (y_array[index] != x_array[ind[k * elem_size + i]]) { in main()
|
| H A D | t219-elemrestriction.c | 11 CeedInt num_elem = 6, elem_size = 2; in main() local
13 CeedInt ind[elem_size * num_elem]; in main()
14 CeedInt8 curl_orients[3 * elem_size * num_elem]; in main()
24 CeedVectorCreate(ceed, num_blk * blk_size * elem_size, &y); in main()
45 …CeedElemRestrictionCreateBlockedCurlOriented(ceed, num_elem, elem_size, blk_size, 1, 1, num_elem +… in main()
55 for (CeedInt i = 0; i < elem_size; i++) { // Node in main()
72 if (y_array[index] != x_array[ind[k * elem_size + i]]) { in main()
|
| H A D | t218-elemrestriction.c | 10 CeedInt num_elem = 6, elem_size = 4; in main() local
11 CeedInt ind[elem_size * num_elem]; in main()
12 CeedInt8 curl_orients[3 * elem_size * num_elem]; in main()
21 CeedVectorCreate(ceed, num_elem * elem_size, &y); in main()
22 CeedVectorCreate(ceed, num_elem * elem_size, &y_unsigned); in main()
62 …CeedElemRestrictionCreateCurlOriented(ceed, num_elem, elem_size, 1, 1, 3 * num_elem + 1, CEED_MEM_… in main()
75 for (CeedInt j = 0; j < elem_size; j++) { in main()
76 CeedInt k = j + elem_size * i; in main()
|
| H A D | t203-elemrestriction.c | 12 CeedInt elem_size = 2; in main() local
16 CeedInt ind[elem_size * num_elem]; in main()
30 CeedVectorCreate(ceed, num_comp * num_blk * blk_size * elem_size, &y); in main()
36 …CeedElemRestrictionCreateBlocked(ceed, num_elem, elem_size, blk_size, num_comp, num_elem + 1, num_… in main()
46 for (CeedInt i = 0; i < elem_size; i++) { // Node in main()
52 if (y_array[index] != x_array[ind[k * elem_size + i] + j * (num_elem + 1)]) { in main()
|
| /libCEED/backends/cuda-ref/ |
| H A D | ceed-cuda-ref-restriction.c | 27 CeedInt num_elem, num_comp, elem_size, comp_stride; in CeedElemRestrictionSetupCompile_Cuda() local
38 CeedCallBackend(CeedElemRestrictionGetMaxPointsInElement(rstr, &elem_size)); in CeedElemRestrictionSetupCompile_Cuda()
40 CeedCallBackend(CeedElemRestrictionGetElementSize(rstr, &elem_size)); in CeedElemRestrictionSetupCompile_Cuda()
49 CeedInt strides[3] = {1, num_elem * elem_size, elem_size}; in CeedElemRestrictionSetupCompile_Cuda()
55 …da(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Cuda()
64 …da(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Cuda()
75 …da(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Cuda()
86 …da(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Cuda()
98 …da(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Cuda()
146 CeedInt elem_size; in CeedElemRestrictionApply_Cuda_Core() local
[all …]
|
| H A D | ceed-cuda-ref-operator.c | 1904 …CeedInt elem_size = 1, num_comp_active = 1, e_vec_size = 0, field_in = impl->input_fie… in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda() local
1919 …f (!is_active_at_points) CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
1920 else elem_size = max_num_points; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
1924 e_vec_size = elem_size * num_comp_active; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
1932 CeedInt node = (s - 1) % elem_size, comp = (s - 1) / elem_size; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
1933 CeedSize start = node * 1 + comp * (elem_size * num_elem); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
1934 CeedSize stop = (comp + 1) * (elem_size * num_elem); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
1936 … (s != 0) CeedCallBackend(CeedVectorSetValueStrided(active_e_vec_in, start, stop, elem_size, 0.0)); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
1938 node = s % elem_size, comp = s / elem_size; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
1939 start = node * 1 + comp * (elem_size * num_elem); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Cuda()
[all …]
|
| /libCEED/backends/hip-ref/ |
| H A D | ceed-hip-ref-restriction.c | 26 CeedInt num_elem, num_comp, elem_size, comp_stride; in CeedElemRestrictionSetupCompile_Hip() local
37 CeedCallBackend(CeedElemRestrictionGetMaxPointsInElement(rstr, &elem_size)); in CeedElemRestrictionSetupCompile_Hip()
39 CeedCallBackend(CeedElemRestrictionGetElementSize(rstr, &elem_size)); in CeedElemRestrictionSetupCompile_Hip()
48 CeedInt strides[3] = {1, num_elem * elem_size, elem_size}; in CeedElemRestrictionSetupCompile_Hip()
54 …ip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Hip()
63 …ip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Hip()
74 …ip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Hip()
85 …ip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Hip()
98 …ip(ceed, restriction_kernel_source, &impl->module, 6, "RSTR_ELEM_SIZE", elem_size, "RSTR_NUM_ELEM"… in CeedElemRestrictionSetupCompile_Hip()
147 CeedInt elem_size; in CeedElemRestrictionApply_Hip_Core() local
[all …]
|
| H A D | ceed-hip-ref-operator.c | 1901 …CeedInt elem_size = 1, num_comp_active = 1, e_vec_size = 0, field_in = impl->input_fie… in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip() local
1916 …f (!is_active_at_points) CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
1917 else elem_size = max_num_points; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
1921 e_vec_size = elem_size * num_comp_active; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
1929 CeedInt node = (s - 1) % elem_size, comp = (s - 1) / elem_size; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
1930 CeedSize start = node * 1 + comp * (elem_size * num_elem); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
1931 CeedSize stop = (comp + 1) * (elem_size * num_elem); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
1933 … (s != 0) CeedCallBackend(CeedVectorSetValueStrided(active_e_vec_in, start, stop, elem_size, 0.0)); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
1935 node = s % elem_size, comp = s / elem_size; in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
1936 start = node * 1 + comp * (elem_size * num_elem); in CeedOperatorLinearAssembleAddDiagonalAtPoints_Hip()
[all …]
|
| /libCEED/python/tests/ |
| H A D | test-2-elemrestriction.py | 81 elem_size = 2
93 r = ceed.BlockedElemRestriction(num_elem, elem_size, blk_size, 1, 1,
96 y = ceed.Vector(num_blk * blk_size * elem_size)
103 for i in range(elem_size):
111 assert y_array[indx] == a[ind[k * elem_size + i]]
129 elem_size = 2
141 r = ceed.BlockedElemRestriction(num_elem, elem_size, blk_size, 1, 1,
144 y = ceed.Vector(blk_size * elem_size)
151 for i in range(elem_size):
158 layout[2] - blk_size * elem_size
[all …]
|
| /libCEED/include/ceed/jit-source/cuda/ |
| H A D | cuda-gen-templates.h | 255 const CeedInt elem_size = P_1D * P_1D; in WriteLVecStandard2d_Assembly() local
256 const CeedInt in_comp = in / elem_size; in WriteLVecStandard2d_Assembly()
258 const CeedInt in_node_y = (in % elem_size) / P_1D; in WriteLVecStandard2d_Assembly()
259 const CeedInt e_vec_size = elem_size * NUM_COMP; in WriteLVecStandard2d_Assembly()
266 …const CeedInt index = (in_comp * NUM_COMP + comp) * elem_size * elem_size + out_node * elem_size +… in WriteLVecStandard2d_Assembly()
421 const CeedInt elem_size = P_1D * P_1D * P_1D; in WriteLVecStandard3d_Assembly() local
422 const CeedInt in_comp = in / elem_size; in WriteLVecStandard3d_Assembly()
425 const CeedInt in_node_z = (in % elem_size) / (P_1D * P_1D); in WriteLVecStandard3d_Assembly()
426 const CeedInt e_vec_size = elem_size * NUM_COMP; in WriteLVecStandard3d_Assembly()
434 …const CeedInt index = (in_comp * NUM_COMP + comp) * elem_size * elem_size + out_node * elem_size +… in WriteLVecStandard3d_Assembly()
|
| /libCEED/include/ceed/jit-source/hip/ |
| H A D | hip-gen-templates.h | 253 const CeedInt elem_size = P_1D * P_1D; in WriteLVecStandard2d_Assembly() local
254 const CeedInt in_comp = in / elem_size; in WriteLVecStandard2d_Assembly()
256 const CeedInt in_node_y = (in % elem_size) / P_1D; in WriteLVecStandard2d_Assembly()
257 const CeedInt e_vec_size = elem_size * NUM_COMP; in WriteLVecStandard2d_Assembly()
264 …const CeedInt index = (in_comp * NUM_COMP + comp) * elem_size * elem_size + out_node * elem_size +… in WriteLVecStandard2d_Assembly()
418 const CeedInt elem_size = P_1D * P_1D * P_1D; in WriteLVecStandard3d_Assembly() local
419 const CeedInt in_comp = in / elem_size; in WriteLVecStandard3d_Assembly()
422 const CeedInt in_node_z = (in % elem_size) / (P_1D * P_1D); in WriteLVecStandard3d_Assembly()
423 const CeedInt e_vec_size = elem_size * NUM_COMP; in WriteLVecStandard3d_Assembly()
431 …const CeedInt index = (in_comp * NUM_COMP + comp) * elem_size * elem_size + out_node * elem_size +… in WriteLVecStandard3d_Assembly()
|
| /libCEED/backends/sycl-gen/ |
| H A D | ceed-sycl-gen-operator-build.sycl.cpp | 66 …CeedInt Q, P_1d = 0, Q_1d = 0, elem_size, num_input_fields, num_output_fields, n… in CeedOperatorBuildKernel_Sycl_gen() local
276 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorBuildKernel_Sycl_gen()
336 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorBuildKernel_Sycl_gen()
403 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorBuildKernel_Sycl_gen()
431 CeedInt strides[3] = {1, elem_size * num_elem, elem_size}; in CeedOperatorBuildKernel_Sycl_gen()
545 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorBuildKernel_Sycl_gen()
548 CeedInt strides[3] = {1, elem_size * num_elem, elem_size}; in CeedOperatorBuildKernel_Sycl_gen()
679 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorBuildKernel_Sycl_gen()
741 CeedInt strides[3] = {1, elem_size * num_elem, elem_size}; in CeedOperatorBuildKernel_Sycl_gen()
|
| /libCEED/backends/blocked/ |
| H A D | ceed-blocked-operator.c | 53 CeedInt num_elem, elem_size, comp_stride; in CeedOperatorSetupFields_Blocked() local
60 CeedCallBackend(CeedElemRestrictionGetElementSize(rstr, &elem_size)); in CeedOperatorSetupFields_Blocked()
71 …CeedCallBackend(CeedElemRestrictionCreateBlocked(ceed_rstr, num_elem, elem_size, block_size, num_c… in CeedOperatorSetupFields_Blocked()
81 …CeedCallBackend(CeedElemRestrictionCreateBlockedOriented(ceed_rstr, num_elem, elem_size, block_siz… in CeedOperatorSetupFields_Blocked()
92 …ckend(CeedElemRestrictionCreateBlockedCurlOriented(ceed_rstr, num_elem, elem_size, block_size, num… in CeedOperatorSetupFields_Blocked()
102 …CeedCallBackend(CeedElemRestrictionCreateBlockedStrided(ceed_rstr, num_elem, elem_size, block_size… in CeedOperatorSetupFields_Blocked()
312 CeedInt elem_size, size, num_comp; in CeedOperatorInputBasis_Blocked() local
330 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorInputBasis_Blocked()
345 …vecs_in[i], CEED_MEM_HOST, CEED_USE_POINTER, &e_data_full[i][(CeedSize)e * elem_size * num_comp])); in CeedOperatorInputBasis_Blocked()
363 CeedInt elem_size, num_comp; in CeedOperatorOutputBasis_Blocked() local
[all …]
|
| /libCEED/include/ceed/ |
| H A D | ceed.h | 262 CEED_EXTERN int CeedElemRestrictionCreate(Ceed ceed, CeedInt num_elem, CeedInt elem_size, CeedInt …
264 CEED_EXTERN int CeedElemRestrictionCreateOriented(Ceed ceed, CeedInt num_elem, CeedInt elem_size, …
267 …dElemRestrictionCreateCurlOriented(Ceed ceed, CeedInt num_elem, CeedInt elem_size, CeedInt num_com…
270 CEED_EXTERN int CeedElemRestrictionCreateStrided(Ceed ceed, CeedInt num_elem, CeedInt elem_size, C…
274 CEED_EXTERN int CeedElemRestrictionCreateBlocked(Ceed ceed, CeedInt num_elem, CeedInt elem_size, C…
277 …emRestrictionCreateBlockedOriented(Ceed ceed, CeedInt num_elem, CeedInt elem_size, CeedInt block_s…
280 …strictionCreateBlockedCurlOriented(Ceed ceed, CeedInt num_elem, CeedInt elem_size, CeedInt block_s…
283 …lemRestrictionCreateBlockedStrided(Ceed ceed, CeedInt num_elem, CeedInt elem_size, CeedInt block_s…
298 CEED_EXTERN int CeedElemRestrictionGetElementSize(CeedElemRestriction rstr, CeedInt *elem_size);
|
| /libCEED/backends/opt/ |
| H A D | ceed-opt-operator.c | 53 CeedInt num_elem, elem_size, comp_stride; in CeedOperatorSetupFields_Opt() local
60 CeedCallBackend(CeedElemRestrictionGetElementSize(rstr, &elem_size)); in CeedOperatorSetupFields_Opt()
71 …CeedCallBackend(CeedElemRestrictionCreateBlocked(ceed_rstr, num_elem, elem_size, block_size, num_c… in CeedOperatorSetupFields_Opt()
81 …CeedCallBackend(CeedElemRestrictionCreateBlockedOriented(ceed_rstr, num_elem, elem_size, block_siz… in CeedOperatorSetupFields_Opt()
92 …ckend(CeedElemRestrictionCreateBlockedCurlOriented(ceed_rstr, num_elem, elem_size, block_size, num… in CeedOperatorSetupFields_Opt()
102 …CeedCallBackend(CeedElemRestrictionCreateBlockedStrided(ceed_rstr, num_elem, elem_size, block_size… in CeedOperatorSetupFields_Opt()
322 CeedInt elem_size, size, num_comp; in CeedOperatorInputBasis_Opt() local
336 CeedCallBackend(CeedElemRestrictionGetElementSize(elem_rstr, &elem_size)); in CeedOperatorInputBasis_Opt()
358 …l->e_vecs_in[i], CEED_MEM_HOST, CEED_USE_POINTER, &e_data[i][(CeedSize)e * elem_size * num_comp])); in CeedOperatorInputBasis_Opt()
|
| /libCEED/examples/fluids/src/ |
| H A D | dm_utils.c | 66 PetscInt num_elem, elem_size, num_dof, num_comp, *restriction_offsets_petsc; in DMPlexCeedElemRestrictionCreate() local
70 …calOffsets(dm, domain_label, label_value, height, dm_field, &num_elem, &elem_size, &num_comp, &num… in DMPlexCeedElemRestrictionCreate()
72 …PetscCall(IntArrayPetscToCeed(num_elem * elem_size, &restriction_offsets_petsc, &restriction_offse… in DMPlexCeedElemRestrictionCreate()
73 …PetscCallCeed(ceed, CeedElemRestrictionCreate(ceed, num_elem, elem_size, num_comp, 1, num_dof, CEE… in DMPlexCeedElemRestrictionCreate()
|