/dports/science/PETSc/petsc-3.14.1/src/ts/utils/dmplexlandau/cuda/ |
H A D | landaucu.cu | 154 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 D | cuda_low.cc | 86 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 D | timer.h | 13 # 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 D | cudacc.cc | 39 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 D | Kokkos_Cuda_Graph_Impl.hpp | 85 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 D | Kokkos_Cuda_Locks.cpp | 85 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 D | Kokkos_CudaSpace.cpp | 95 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 D | Kokkos_Cuda_Task.hpp | 252 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 D | Kokkos_Cuda_Graph_Impl.hpp | 85 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 D | Kokkos_Cuda_Locks.cpp | 85 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 D | Kokkos_CudaSpace.cpp | 95 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 D | Kokkos_Cuda_Task.hpp | 252 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 D | Kokkos_Cuda_Graph_Impl.hpp | 85 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 D | Kokkos_Cuda_Locks.cpp | 85 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 D | Kokkos_CudaSpace.cpp | 95 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 D | Kokkos_Cuda_Task.hpp | 252 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 D | test.cu | 8 # 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 D | cuda_wrapper.cu | 111 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 D | TestCuda_InterOp_Init.cpp | 63 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 D | TestCuda_InterOp_Init.cpp | 63 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 D | TestCuda_InterOp_Init.cpp | 63 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 D | cuda_array_wrapper.h | 126 CUDA_SAFE_CALL(cudaMemcpy3D(¶ms)); in CopyToDevice() 137 CUDA_SAFE_CALL(cudaMemcpy3D(¶ms)); in CopyToHost() 149 CUDA_SAFE_CALL(cudaMemcpy3D(¶meters)); 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 D | radixsort_app.cu | 891 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 D | radixsort_app.cu | 891 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 D | allocate_hardware_aware.cc | 29 #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()
|