Home
last modified time | relevance | path

Searched refs:CUDA_SAFE_CALL (Results 1 – 25 of 55) sorted by relevance

123

/dports/science/PETSc/petsc-3.14.1/src/ts/utils/dmplexlandau/cuda/
H A Dlandaucu.cu154 CUDA_SAFE_CALL(cudaFree(d_g2g3)); in LandauCUDAJacobian()
161 CUDA_SAFE_CALL(cudaFree(d_invJj)); in LandauCUDAJacobian()
164 CUDA_SAFE_CALL(cudaFree(d_nu_beta)); in LandauCUDAJacobian()
166 CUDA_SAFE_CALL(cudaFree(d_Eq_m)); in LandauCUDAJacobian()
167 CUDA_SAFE_CALL(cudaFree(d_BB)); in LandauCUDAJacobian()
168 CUDA_SAFE_CALL(cudaFree(d_DD)); in LandauCUDAJacobian()
314 CUDA_SAFE_CALL(cudaFree(d_colors)); in LandauAssembleCuda()
338 CUDA_SAFE_CALL(cudaFree(a->i)); in LandauAssembleCuda()
340 CUDA_SAFE_CALL(cudaFree(a->j)); in LandauAssembleCuda()
341 CUDA_SAFE_CALL(cudaFree(a->a)); in LandauAssembleCuda()
[all …]
/dports/science/octopus/octopus-10.5/src/basic/
H A Dcuda_low.cc86 CUDA_SAFE_CALL(cuInit(0)); in FC_FUNC_()
93 CUDA_SAFE_CALL(cuDeviceGetCount(&ndevices)); in FC_FUNC_()
101 CUDA_SAFE_CALL(cuDeviceGet(*device, *device_number)); in FC_FUNC_()
103 CUDA_SAFE_CALL(cuCtxCreate(*context, 0, **device)); in FC_FUNC_()
120 CUDA_SAFE_CALL(cuCtxDestroy(**context)); in FC_FUNC_()
136 CUDA_SAFE_CALL(cuModuleUnload(*module)); in FC_FUNC_()
278 CUDA_SAFE_CALL(cuModuleUnload(**module)); in FC_FUNC_()
300 CUDA_SAFE_CALL(cuDeviceTotalMem(&mem, **device)); in FC_FUNC_()
316 CUDA_SAFE_CALL(cuMemAlloc(*cuda_ptr, *size)); in FC_FUNC_()
322 CUDA_SAFE_CALL(cuMemFree(**cuda_ptr)); in FC_FUNC_()
[all …]
/dports/devel/thrust/thrust-1.9.5/internal/benchmark/
H A Dtimer.h13 # define CUDA_SAFE_CALL( call) do { \ macro
30 CUDA_SAFE_CALL(cudaEventCreate(&start_)); in cuda_timer()
31 CUDA_SAFE_CALL(cudaEventCreate(&stop_)); in cuda_timer()
36 CUDA_SAFE_CALL(cudaEventDestroy(start_)); in ~cuda_timer()
37 CUDA_SAFE_CALL(cudaEventDestroy(stop_)); in ~cuda_timer()
42 CUDA_SAFE_CALL(cudaEventRecord(start_, 0)); in start()
47 CUDA_SAFE_CALL(cudaEventRecord(stop_, 0)); in stop()
48 CUDA_SAFE_CALL(cudaEventSynchronize(stop_)); in stop()
54 CUDA_SAFE_CALL(cudaEventElapsedTime(&elapsed_time, start_, stop_)); in milliseconds_elapsed()
/dports/graphics/colmap/colmap-3.6/src/util/
H A Dcudacc.cc39 CUDA_SAFE_CALL(cudaEventCreate(&start_)); in CudaTimer()
40 CUDA_SAFE_CALL(cudaEventCreate(&stop_)); in CudaTimer()
41 CUDA_SAFE_CALL(cudaEventRecord(start_, 0)); in CudaTimer()
45 CUDA_SAFE_CALL(cudaEventDestroy(start_)); in ~CudaTimer()
46 CUDA_SAFE_CALL(cudaEventDestroy(stop_)); in ~CudaTimer()
50 CUDA_SAFE_CALL(cudaEventRecord(stop_, 0)); in Print()
51 CUDA_SAFE_CALL(cudaEventSynchronize(stop_)); in Print()
52 CUDA_SAFE_CALL(cudaEventElapsedTime(&elapsed_time_, start_, stop_)); in Print()
/dports/science/lammps/lammps-stable_29Sep2021/lib/kokkos/core/src/Cuda/
H A DKokkos_Cuda_Graph_Impl.hpp85 CUDA_SAFE_CALL(cudaGraphInstantiate(&m_graph_exec, m_graph, &error_node, in _instantiate_graph()
113 CUDA_SAFE_CALL(cudaGraphExecDestroy(m_graph_exec)); in ~GraphImpl()
115 CUDA_SAFE_CALL(cudaGraphDestroy(m_graph)); in ~GraphImpl()
120 CUDA_SAFE_CALL(cudaGraphCreate(&m_graph, cuda_graph_flags_t{0})); in GraphImpl()
126 CUDA_SAFE_CALL(cudaGraphAddEmptyNode(&(arg_node_ptr->node_details_t::node), in add_node()
174 CUDA_SAFE_CALL( in add_predecessor()
182 CUDA_SAFE_CALL( in submit()
195 CUDA_SAFE_CALL(cudaGraphAddEmptyNode(&(rv->node_details_t::node), m_graph, in create_root_node_ptr()
H A DKokkos_Cuda_Locks.cpp85 CUDA_SAFE_CALL(cudaMalloc(&g_host_cuda_lock_arrays.atomic, in initialize_host_cuda_lock_arrays()
87 CUDA_SAFE_CALL(cudaMalloc(&g_host_cuda_lock_arrays.scratch, in initialize_host_cuda_lock_arrays()
89 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in initialize_host_cuda_lock_arrays()
96 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in initialize_host_cuda_lock_arrays()
H A DKokkos_CudaSpace.cpp95 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
100 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
105 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
110 CUDA_SAFE_CALL( in DeepCopy()
116 CUDA_SAFE_CALL( in DeepCopy()
122 CUDA_SAFE_CALL( in DeepCopy()
342 CUDA_SAFE_CALL(cudaFree(arg_alloc_ptr)); in impl_deallocate()
375 CUDA_SAFE_CALL(cudaFree(arg_alloc_ptr)); in impl_deallocate()
404 CUDA_SAFE_CALL(cudaFreeHost(arg_alloc_ptr)); in impl_deallocate()
465 CUDA_SAFE_CALL( in attach_texture_object()
[all …]
H A DKokkos_Cuda_Task.hpp252 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in execute()
257 CUDA_SAFE_CALL( in execute()
271 CUDA_SAFE_CALL(cudaGetLastError()); in execute()
273 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in execute()
276 CUDA_SAFE_CALL( in execute()
298 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in get_function_pointer()
303 CUDA_SAFE_CALL(cudaGetLastError()); in get_function_pointer()
483 CUDA_SAFE_CALL( in execute()
497 CUDA_SAFE_CALL(cudaGetLastError()); in execute()
502 CUDA_SAFE_CALL( in execute()
[all …]
/dports/devel/kokkos/kokkos-3.4.01/core/src/Cuda/
H A DKokkos_Cuda_Graph_Impl.hpp85 CUDA_SAFE_CALL(cudaGraphInstantiate(&m_graph_exec, m_graph, &error_node, in _instantiate_graph()
113 CUDA_SAFE_CALL(cudaGraphExecDestroy(m_graph_exec)); in ~GraphImpl()
115 CUDA_SAFE_CALL(cudaGraphDestroy(m_graph)); in ~GraphImpl()
120 CUDA_SAFE_CALL(cudaGraphCreate(&m_graph, cuda_graph_flags_t{0})); in GraphImpl()
126 CUDA_SAFE_CALL(cudaGraphAddEmptyNode(&(arg_node_ptr->node_details_t::node), in add_node()
174 CUDA_SAFE_CALL( in add_predecessor()
182 CUDA_SAFE_CALL( in submit()
195 CUDA_SAFE_CALL(cudaGraphAddEmptyNode(&(rv->node_details_t::node), m_graph, in create_root_node_ptr()
H A DKokkos_Cuda_Locks.cpp85 CUDA_SAFE_CALL(cudaMalloc(&g_host_cuda_lock_arrays.atomic, in initialize_host_cuda_lock_arrays()
87 CUDA_SAFE_CALL(cudaMalloc(&g_host_cuda_lock_arrays.scratch, in initialize_host_cuda_lock_arrays()
89 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in initialize_host_cuda_lock_arrays()
96 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in initialize_host_cuda_lock_arrays()
H A DKokkos_CudaSpace.cpp95 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
100 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
105 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
110 CUDA_SAFE_CALL( in DeepCopy()
116 CUDA_SAFE_CALL( in DeepCopy()
122 CUDA_SAFE_CALL( in DeepCopy()
342 CUDA_SAFE_CALL(cudaFree(arg_alloc_ptr)); in impl_deallocate()
375 CUDA_SAFE_CALL(cudaFree(arg_alloc_ptr)); in impl_deallocate()
404 CUDA_SAFE_CALL(cudaFreeHost(arg_alloc_ptr)); in impl_deallocate()
465 CUDA_SAFE_CALL( in attach_texture_object()
[all …]
H A DKokkos_Cuda_Task.hpp252 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in execute()
257 CUDA_SAFE_CALL( in execute()
271 CUDA_SAFE_CALL(cudaGetLastError()); in execute()
273 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in execute()
276 CUDA_SAFE_CALL( in execute()
298 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in get_function_pointer()
303 CUDA_SAFE_CALL(cudaGetLastError()); in get_function_pointer()
483 CUDA_SAFE_CALL( in execute()
497 CUDA_SAFE_CALL(cudaGetLastError()); in execute()
502 CUDA_SAFE_CALL( in execute()
[all …]
/dports/science/sparta/sparta-20Oct2021/lib/kokkos/core/src/Cuda/
H A DKokkos_Cuda_Graph_Impl.hpp85 CUDA_SAFE_CALL(cudaGraphInstantiate(&m_graph_exec, m_graph, &error_node, in _instantiate_graph()
113 CUDA_SAFE_CALL(cudaGraphExecDestroy(m_graph_exec)); in ~GraphImpl()
115 CUDA_SAFE_CALL(cudaGraphDestroy(m_graph)); in ~GraphImpl()
120 CUDA_SAFE_CALL(cudaGraphCreate(&m_graph, cuda_graph_flags_t{0})); in GraphImpl()
126 CUDA_SAFE_CALL(cudaGraphAddEmptyNode(&(arg_node_ptr->node_details_t::node), in add_node()
174 CUDA_SAFE_CALL( in add_predecessor()
182 CUDA_SAFE_CALL( in submit()
195 CUDA_SAFE_CALL(cudaGraphAddEmptyNode(&(rv->node_details_t::node), m_graph, in create_root_node_ptr()
H A DKokkos_Cuda_Locks.cpp85 CUDA_SAFE_CALL(cudaMalloc(&g_host_cuda_lock_arrays.atomic, in initialize_host_cuda_lock_arrays()
87 CUDA_SAFE_CALL(cudaMalloc(&g_host_cuda_lock_arrays.scratch, in initialize_host_cuda_lock_arrays()
89 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in initialize_host_cuda_lock_arrays()
96 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in initialize_host_cuda_lock_arrays()
H A DKokkos_CudaSpace.cpp95 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
100 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
105 CUDA_SAFE_CALL(cudaMemcpy(dst, src, n, cudaMemcpyDefault)); in DeepCopy()
110 CUDA_SAFE_CALL( in DeepCopy()
116 CUDA_SAFE_CALL( in DeepCopy()
122 CUDA_SAFE_CALL( in DeepCopy()
342 CUDA_SAFE_CALL(cudaFree(arg_alloc_ptr)); in impl_deallocate()
375 CUDA_SAFE_CALL(cudaFree(arg_alloc_ptr)); in impl_deallocate()
404 CUDA_SAFE_CALL(cudaFreeHost(arg_alloc_ptr)); in impl_deallocate()
465 CUDA_SAFE_CALL( in attach_texture_object()
[all …]
H A DKokkos_Cuda_Task.hpp252 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in execute()
257 CUDA_SAFE_CALL( in execute()
271 CUDA_SAFE_CALL(cudaGetLastError()); in execute()
273 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in execute()
276 CUDA_SAFE_CALL( in execute()
298 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in get_function_pointer()
303 CUDA_SAFE_CALL(cudaGetLastError()); in get_function_pointer()
483 CUDA_SAFE_CALL( in execute()
497 CUDA_SAFE_CALL(cudaGetLastError()); in execute()
502 CUDA_SAFE_CALL( in execute()
[all …]
/dports/multimedia/mpv/waf-2.0.20/playground/cuda/
H A Dtest.cu8 # define CUDA_SAFE_CALL( call) { \ macro
42 CUDA_SAFE_CALL( cudaMalloc((void **) &recf, SIZ * sizeof(unsigned int)) ); in testcuda()
43 CUDA_SAFE_CALL(cudaMemcpy(recf, foo, SIZ * sizeof(unsigned int), cudaMemcpyHostToDevice)); in testcuda()
46 CUDA_SAFE_CALL(cudaMemcpy(foo, recf, SIZ * sizeof(unsigned int), cudaMemcpyDeviceToHost)); in testcuda() local
49 CUDA_SAFE_CALL(cudaFree(recf)); in testcuda()
/dports/science/liggghts/LIGGGHTS-PUBLIC-3.8.0-26-g6e873439/lib/cuda/
H A Dcuda_wrapper.cu111 CUDA_SAFE_CALL(cudaSetDevice(devicea)); in CudaWrapper_Init()
113 CUDA_SAFE_CALL(cudaSetValidDevices(dev_list, deviceCount)); in CudaWrapper_Init()
119 CUDA_SAFE_CALL(cudaGetDevice(&dev)); in CudaWrapper_Init()
168 CUDA_SAFE_CALL(cudaMalloc((void**)&dev_data, nbytes)); in CudaWrapper_AllocCudaData()
180 CUDA_SAFE_CALL(cudaMemcpy(dev_data, host_data, nbytes, cudaMemcpyHostToDevice)); in CudaWrapper_UploadCudaData()
198 CUDA_SAFE_CALL(cudaMemcpy(host_data, dev_data, nbytes, cudaMemcpyDeviceToHost)); in CudaWrapper_DownloadCudaData()
213 CUDA_SAFE_CALL(cudaFree(dev_data)); in CudaWrapper_FreeCudaData()
220 CUDA_SAFE_CALL(cudaMemset(dev_data, value, nbytes)); in CudaWrapper_Memset()
226 CUDA_SAFE_CALL(cudaMemcpy(dev_dest, dev_source, nbytes, cudaMemcpyDeviceToDevice)); in CudaWrapper_CopyData()
238 CUDA_SAFE_CALL(cudaHostAlloc((void**)&host_data, nbytes, flags)); in CudaWrapper_AllocPinnedHostData()
[all …]
/dports/science/lammps/lammps-stable_29Sep2021/lib/kokkos/core/unit_test/cuda/
H A DTestCuda_InterOp_Init.cpp63 CUDA_SAFE_CALL(cudaMalloc(&p, sizeof(int) * 100)); in TEST()
73 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in TEST()
77 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in TEST()
86 CUDA_SAFE_CALL(cudaFree(p)); in TEST()
/dports/devel/kokkos/kokkos-3.4.01/core/unit_test/cuda/
H A DTestCuda_InterOp_Init.cpp63 CUDA_SAFE_CALL(cudaMalloc(&p, sizeof(int) * 100)); in TEST()
73 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in TEST()
77 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in TEST()
86 CUDA_SAFE_CALL(cudaFree(p)); in TEST()
/dports/science/sparta/sparta-20Oct2021/lib/kokkos/core/unit_test/cuda/
H A DTestCuda_InterOp_Init.cpp63 CUDA_SAFE_CALL(cudaMalloc(&p, sizeof(int) * 100)); in TEST()
73 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in TEST()
77 CUDA_SAFE_CALL(cudaDeviceSynchronize()); in TEST()
86 CUDA_SAFE_CALL(cudaFree(p)); in TEST()
/dports/graphics/colmap/colmap-3.6/src/mvs/
H A Dcuda_array_wrapper.h126 CUDA_SAFE_CALL(cudaMemcpy3D(&params)); in CopyToDevice()
137 CUDA_SAFE_CALL(cudaMemcpy3D(&params)); in CopyToHost()
149 CUDA_SAFE_CALL(cudaMemcpy3D(&parameters)); in CopyFromGpuMat()
157 CUDA_SAFE_CALL(cudaMalloc3DArray(&array_, &fmt, extent, cudaArrayLayered)); in Allocate()
163 CUDA_SAFE_CALL(cudaFreeArray(array_)); in Deallocate()
/dports/science/lammps/lammps-stable_29Sep2021/lib/gpu/cudpp_mini/
H A Dradixsort_app.cu891 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_tempKeys, in allocRadixSortStorage()
898 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_counters, in allocRadixSortStorage()
901 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_countersSum, in allocRadixSortStorage()
909 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_tempKeys, in allocRadixSortStorage()
916 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_counters, in allocRadixSortStorage()
919 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_countersSum, in allocRadixSortStorage()
938 CUDA_SAFE_CALL( cudaFree(plan->m_tempKeys)); in freeRadixSortStorage()
939 CUDA_SAFE_CALL( cudaFree(plan->m_tempValues)); in freeRadixSortStorage()
940 CUDA_SAFE_CALL( cudaFree(plan->m_counters)); in freeRadixSortStorage()
941 CUDA_SAFE_CALL( cudaFree(plan->m_countersSum)); in freeRadixSortStorage()
[all …]
/dports/science/liggghts/LIGGGHTS-PUBLIC-3.8.0-26-g6e873439/lib/gpu/cudpp_mini/
H A Dradixsort_app.cu891 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_tempKeys, in allocRadixSortStorage()
898 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_counters, in allocRadixSortStorage()
901 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_countersSum, in allocRadixSortStorage()
909 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_tempKeys, in allocRadixSortStorage()
916 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_counters, in allocRadixSortStorage()
919 CUDA_SAFE_CALL(cudaMalloc((void **)&plan->m_countersSum, in allocRadixSortStorage()
938 CUDA_SAFE_CALL( cudaFree(plan->m_tempKeys)); in freeRadixSortStorage()
939 CUDA_SAFE_CALL( cudaFree(plan->m_tempValues)); in freeRadixSortStorage()
940 CUDA_SAFE_CALL( cudaFree(plan->m_counters)); in freeRadixSortStorage()
941 CUDA_SAFE_CALL( cudaFree(plan->m_countersSum)); in freeRadixSortStorage()
[all …]
/dports/science/octopus/octopus-10.5/src/grid/
H A Dallocate_hardware_aware.cc29 #define CUDA_SAFE_CALL(x) \ macro
89 CUDA_SAFE_CALL(cuMemAllocHost(&pinned, (unsigned int)size_bytes)); in allocate_pinned()
118 CUDA_SAFE_CALL(cuMemFreeHost(array)); in deallocate_pinned()

123