    

 ## On this page

  

 

 # api\_backend

 Last update: 17.07.2025 

<a id="l00001" name="l00001"></a> 1\#pragma once

<a id="l00002" name="l00002"></a> 2 

<a id="l00003" name="l00003"></a> 3\#ifdef \_\_CUDA\_ARCH\_\_

<a id="l00004" name="l00004"></a> 4\#include &lt;rocky20/cuda/cuda\_backend.hpp&gt;

<a id="l00005" name="l00005"></a> 5\#else

<a id="l00006" name="l00006"></a> 6\#include &lt;rocky20/device/omp\_backend.hpp&gt;

<a id="l00007" name="l00007"></a> 7\#endif

<a id="l00008" name="l00008"></a> 8 

<a id="l00009" name="l00009"></a> 9namespace backend

<a id="l00010" name="l00010"></a> 10{

<a id="l00011" name="l00011"></a> 11 

<a id="l00012" name="l00012"></a> 12template &lt;typename T&gt;

<a id="l00013" name="l00013"></a> 13__host__ __device__ void atomic_add(T *address, T val)

<a id="l00014" name="l00014"></a> 14{

<a id="l00015" name="l00015"></a> 15\#ifdef \_\_CUDA\_ARCH\_\_

<a id="l00016" name="l00016"></a> 16 CudaBackend::AtomicAdd(address, val);

<a id="l00017" name="l00017"></a> 17\#else

<a id="l00018" name="l00018"></a> 18 OMPBackend::AtomicAdd(address, val);

<a id="l00019" name="l00019"></a> 19\#endif

<a id="l00020" name="l00020"></a> 20}

<a id="l00021" name="l00021"></a> 21 

<a id="l00022" name="l00022"></a> 22template &lt;typename T&gt;

<a id="l00023" name="l00023"></a> 23__host__ __device__ void atomic_add(T *address, T val, T &amp;current_value)

<a id="l00024" name="l00024"></a> 24{

<a id="l00025" name="l00025"></a> 25\#ifdef \_\_CUDA\_ARCH\_\_

<a id="l00026" name="l00026"></a> 26 CudaBackend::AtomicAdd(address, val, current_value);

<a id="l00027" name="l00027"></a> 27\#else

<a id="l00028" name="l00028"></a> 28 OMPBackend::AtomicAdd(address, val, current_value);

<a id="l00029" name="l00029"></a> 29\#endif

<a id="l00030" name="l00030"></a> 30}

<a id="l00031" name="l00031"></a> 31 

<a id="l00032" name="l00032"></a> 32template &lt;typename T&gt;

<a id="l00033" name="l00033"></a> 33__host__ __device__ void atomic_max(T* address, T val)

<a id="l00034" name="l00034"></a> 34{

<a id="l00035" name="l00035"></a> 35\#ifdef \_\_CUDA\_ARCH\_\_

<a id="l00036" name="l00036"></a> 36 CudaBackend::AtomicMax(address, val);

<a id="l00037" name="l00037"></a> 37\#else

<a id="l00038" name="l00038"></a> 38 OMPBackend::AtomicMax(address, val);

<a id="l00039" name="l00039"></a> 39\#endif

<a id="l00040" name="l00040"></a> 40}

<a id="l00041" name="l00041"></a> 41 

<a id="l00042" name="l00042"></a> 42}