Commit ff3de5b1 authored by anagainaru's avatar anagainaru
Browse files

Add SYCL specific functions 



Co-authored-by: default avatarDaniel Arndt <arndtd@ornl.gov>
parent 05fe91bf

CMakeLists.txt

+1 −1
Original line number Diff line number Diff line
@@ -237,7 +237,7 @@ endif() 
set(ADIOS2_CONFIG_OPTS

    BP5 DataMan DataSpaces HDF5 HDF5_VOL MHS SST Fortran MPI Python Blosc2

    BZip2 LIBPRESSIO MGARD PNG SZ ZFP DAOS IME O_DIRECT Sodium Catalyst SysVShMem UCX ZeroMQ 

    Profiling Endian_Reverse AWSSDK GPU_Support CUDA Kokkos Kokkos_CUDA Kokkos_HIP

    Profiling Endian_Reverse AWSSDK GPU_Support CUDA Kokkos Kokkos_CUDA Kokkos_HIP Kokkos_SYCL

)



GenerateADIOSHeaderConfig(${ADIOS2_CONFIG_OPTS})

cmake/DetectOptions.cmake

+3 −0
Original line number Diff line number Diff line
@@ -192,6 +192,9 @@ if(ADIOS2_USE_Kokkos) 
        set(ADIOS2_HAVE_Kokkos_HIP TRUE)

        enable_language(HIP)

      endif()

      if(Kokkos_ENABLE_SYCL)

	    set(ADIOS2_HAVE_Kokkos_SYCL TRUE)

      endif()

      set(ADIOS2_HAVE_GPU_Support TRUE)

    endif()

  endif()

source/adios2/helper/kokkos/adiosKokkos.cpp

+10 −0
Original line number Diff line number Diff line
@@ -92,6 +92,15 @@ bool IsGPUbuffer(const void *ptr) 
    {

        return true;

    }

#endif

#ifdef ADIOS2_HAVE_KOKKOS_SYCL

    auto ret =

        sycl::address_space_cast<sycl::access::address_space::global_space,

                                 sycl::access::decorated::no>(ptr);

    if (ret != nullptr)

    {

        return true;

    }

#endif

    return false;

}
@@ -115,6 +124,7 @@ void KokkosInit() 
        settings.set_device_id(device_id);

    }

#endif

    // GetDevice not supported for SYCL, use the default device

    Kokkos::initialize(settings);

}