Merge pull request #158 from psychocoderHPC/topic-hipSupport

add HIP support

Author: PrometheusPi

lib/isaac.hpp

@@ -2257,6 +2257,8 @@ namespace isaac
                    ISAAC_IDX_TYPE((readbackViewport[3] + blockSize.y - 1) / blockSize.y)};
 #if ALPAKA_ACC_GPU_CUDA_ENABLED == 1
             if(boost::mpl::not_<boost::is_same<T_Acc, alpaka::AccGpuCudaRt<T_AccDim, ISAAC_IDX_TYPE>>>::value)
+#elif ALPAKA_ACC_GPU_HIP_ENABLED == 1
+            if(boost::mpl::not_<boost::is_same<T_Acc, alpaka::AccGpuHipRt<T_AccDim, ISAAC_IDX_TYPE>>>::value)
 #endif
             {
                 gridSize.x = ISAAC_IDX_TYPE(readbackViewport[2]);

lib/isaac/isaac_defines.hpp

@@ -53,7 +53,7 @@
 #define ISAAC_Z_NEAR 0.002f
 #define ISAAC_Z_FAR 100.0f
 
-#ifdef __CUDACC__
+#if(BOOST_LANG_CUDA || BOOST_LANG_HIP)
 #    define ISAAC_HOST_DEVICE_INLINE ALPAKA_FN_HOST_ACC __forceinline__
 #else
 #    define ISAAC_HOST_DEVICE_INLINE ALPAKA_FN_HOST_ACC inline
@@ -64,7 +64,7 @@
 
 #define ISAAC_DEVICE_INLINE ISAAC_HOST_DEVICE_INLINE
 
-#ifdef __CUDACC__
+#if(BOOST_LANG_CUDA || BOOST_LANG_HIP)
 #    define ISAAC_DEVICE __device__ __host__
 #else
 #    define ISAAC_DEVICE
@@ -78,7 +78,7 @@
 
 #define ISAAC_CONSTANT ALPAKA_STATIC_ACC_MEM_CONSTANT
 
-#ifdef __CUDACC__
+#if(BOOST_LANG_CUDA || BOOST_LANG_HIP)
 #    define ISAAC_MAX max
 #    define ISAAC_MIN min
 #else

lib/isaac/isaac_kernel.hpp

@@ -53,6 +53,8 @@ namespace isaac
 
 #if ALPAKA_ACC_GPU_CUDA_ENABLED == 1
         if(boost::mpl::not_<boost::is_same<T_Acc, alpaka::AccGpuCudaRt<Dim, ISAAC_IDX_TYPE>>>::value)
+#elif ALPAKA_ACC_GPU_HIP_ENABLED == 1
+        if(boost::mpl::not_<boost::is_same<T_Acc, alpaka::AccGpuHipRt<Dim, ISAAC_IDX_TYPE>>>::value)
 #endif
         {
             blockSize = isaac_size3(1);