| /libCEED/include/ceed/jit-source/cuda/ |
| H A D | cuda-ref-basis-tensor-at-points.h | 43 …l__ void InterpAtPoints(const CeedInt num_elem, const CeedScalar *__restrict__ chebyshev_interp_1d, in InterpAtPoints() argument
55 s_chebyshev_interp_1d[k] = chebyshev_interp_1d[k]; in InterpAtPoints()
126 …InterpTransposeAtPoints(const CeedInt num_elem, const CeedScalar *__restrict__ chebyshev_interp_1d, in InterpTransposeAtPoints() argument
138 s_chebyshev_interp_1d[k] = chebyshev_interp_1d[k]; in InterpTransposeAtPoints()
222 …bal__ void GradAtPoints(const CeedInt num_elem, const CeedScalar *__restrict__ chebyshev_interp_1d, in GradAtPoints() argument
234 s_chebyshev_interp_1d[k] = chebyshev_interp_1d[k]; in GradAtPoints()
311 …d GradTransposeAtPoints(const CeedInt num_elem, const CeedScalar *__restrict__ chebyshev_interp_1d, in GradTransposeAtPoints() argument
323 s_chebyshev_interp_1d[k] = chebyshev_interp_1d[k]; in GradTransposeAtPoints()
|
| /libCEED/include/ceed/jit-source/hip/ |
| H A D | hip-ref-basis-tensor-at-points.h | 43 …l__ void InterpAtPoints(const CeedInt num_elem, const CeedScalar *__restrict__ chebyshev_interp_1d, in InterpAtPoints() argument
55 s_chebyshev_interp_1d[k] = chebyshev_interp_1d[k]; in InterpAtPoints()
126 …InterpTransposeAtPoints(const CeedInt num_elem, const CeedScalar *__restrict__ chebyshev_interp_1d, in InterpTransposeAtPoints() argument
138 s_chebyshev_interp_1d[k] = chebyshev_interp_1d[k]; in InterpTransposeAtPoints()
222 …bal__ void GradAtPoints(const CeedInt num_elem, const CeedScalar *__restrict__ chebyshev_interp_1d, in GradAtPoints() argument
234 s_chebyshev_interp_1d[k] = chebyshev_interp_1d[k]; in GradAtPoints()
311 …d GradTransposeAtPoints(const CeedInt num_elem, const CeedScalar *__restrict__ chebyshev_interp_1d, in GradTransposeAtPoints() argument
323 s_chebyshev_interp_1d[k] = chebyshev_interp_1d[k]; in GradTransposeAtPoints()
|
| /libCEED/backends/hip-ref/ |
| H A D | ceed-hip-ref-basis.c | 167 CeedScalar *chebyshev_interp_1d; in CeedBasisApplyAtPointsCore_Hip() local
170 CeedCallBackend(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Hip()
171 CeedCallBackend(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Hip()
173 …CeedCallHip(ceed, hipMemcpy(data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, hipMem… in CeedBasisApplyAtPointsCore_Hip()
174 CeedCallBackend(CeedFree(&chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Hip()
|
| /libCEED/backends/cuda-ref/ |
| H A D | ceed-cuda-ref-basis.c | 168 CeedScalar *chebyshev_interp_1d; in CeedBasisApplyAtPointsCore_Cuda() local
171 CeedCallBackend(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Cuda()
172 CeedCallBackend(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Cuda()
174 …CeedCallCuda(ceed, cudaMemcpy(data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, cuda… in CeedBasisApplyAtPointsCore_Cuda()
175 CeedCallBackend(CeedFree(&chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Cuda()
|
| /libCEED/backends/hip-shared/ |
| H A D | ceed-hip-shared-basis.c | 341 CeedScalar *chebyshev_interp_1d; in CeedBasisApplyAtPointsCore_Hip_shared() local
344 CeedCallBackend(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Hip_shared()
345 CeedCallBackend(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Hip_shared()
347 …CeedCallHip(ceed, hipMemcpy(data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, hipMem… in CeedBasisApplyAtPointsCore_Hip_shared()
348 CeedCallBackend(CeedFree(&chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Hip_shared()
|
| /libCEED/backends/cuda-shared/ |
| H A D | ceed-cuda-shared-basis.c | 276 CeedScalar *chebyshev_interp_1d; in CeedBasisApplyAtPointsCore_Cuda_shared() local
279 CeedCallBackend(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Cuda_shared()
280 CeedCallBackend(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Cuda_shared()
282 …CeedCallCuda(ceed, cudaMemcpy(data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, cuda… in CeedBasisApplyAtPointsCore_Cuda_shared()
283 CeedCallBackend(CeedFree(&chebyshev_interp_1d)); in CeedBasisApplyAtPointsCore_Cuda_shared()
|
| /libCEED/backends/hip-gen/ |
| H A D | ceed-hip-gen-operator-build.cpp | 277 CeedScalar *chebyshev_interp_1d; in CeedOperatorBuildKernelFieldData_Hip_gen() local
280 CeedCallBackend(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Hip_gen()
281 CeedCallBackend(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Hip_gen()
284 …hipMemcpy(basis_data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, hipMemcpyHostToDev… in CeedOperatorBuildKernelFieldData_Hip_gen()
285 CeedCallBackend(CeedFree(&chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Hip_gen()
315 CeedScalar *chebyshev_interp_1d; in CeedOperatorBuildKernelFieldData_Hip_gen() local
318 CeedCallBackend(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Hip_gen()
319 CeedCallBackend(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Hip_gen()
322 …hipMemcpy(basis_data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, hipMemcpyHostToDev… in CeedOperatorBuildKernelFieldData_Hip_gen()
323 CeedCallBackend(CeedFree(&chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Hip_gen()
|
| /libCEED/backends/cuda-gen/ |
| H A D | ceed-cuda-gen-operator-build.cpp | 250 CeedScalar *chebyshev_interp_1d; in CeedOperatorBuildKernelFieldData_Cuda_gen() local
253 CeedCallBackend(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Cuda_gen()
254 CeedCallBackend(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Cuda_gen()
257 …cudaMemcpy(basis_data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, cudaMemcpyHostToD… in CeedOperatorBuildKernelFieldData_Cuda_gen()
258 CeedCallBackend(CeedFree(&chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Cuda_gen()
288 CeedScalar *chebyshev_interp_1d; in CeedOperatorBuildKernelFieldData_Cuda_gen() local
291 CeedCallBackend(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Cuda_gen()
292 CeedCallBackend(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Cuda_gen()
295 …cudaMemcpy(basis_data->d_chebyshev_interp_1d, chebyshev_interp_1d, interp_bytes, cudaMemcpyHostToD… in CeedOperatorBuildKernelFieldData_Cuda_gen()
296 CeedCallBackend(CeedFree(&chebyshev_interp_1d)); in CeedOperatorBuildKernelFieldData_Cuda_gen()
|
| /libCEED/interface/ |
| H A D | ceed-basis.c | 503 CeedScalar *chebyshev_interp_1d, *chebyshev_grad_1d, *chebyshev_q_weight_1d; in CeedBasisApplyAtPoints_Core() local
507 CeedCall(CeedCalloc(P_1d * Q_1d, &chebyshev_interp_1d)); in CeedBasisApplyAtPoints_Core()
511 CeedCall(CeedBasisGetChebyshevInterp1D(basis, chebyshev_interp_1d)); in CeedBasisApplyAtPoints_Core()
515 …CeedCall(CeedBasisCreateTensorH1(ceed, dim, num_comp, P_1d, Q_1d, chebyshev_interp_1d, chebyshev_g… in CeedBasisApplyAtPoints_Core()
519 CeedCall(CeedFree(&chebyshev_interp_1d)); in CeedBasisApplyAtPoints_Core()
766 int CeedBasisGetChebyshevInterp1D(CeedBasis basis, CeedScalar *chebyshev_interp_1d) { in CeedBasisGetChebyshevInterp1D() argument
789 …CeedCall(CeedMatrixMatrixMultiply(ceed, chebyshev_coeffs_1d_inv, interp_1d, chebyshev_interp_1d, Q… in CeedBasisGetChebyshevInterp1D()
|
| /libCEED/include/ceed/ |
| H A D | backend.h | 343 CEED_EXTERN int CeedBasisGetChebyshevInterp1D(CeedBasis basis, CeedScalar *chebyshev_interp_1d);
|