2 # This file is part of the GROMACS molecular simulation package.
4 # Copyright (c) 2020,2021, by the GROMACS development team, led by
5 # Mark Abraham, David van der Spoel, Berk Hess, and Erik Lindahl,
6 # and including many others, as listed in the AUTHORS file in the
7 # top-level source directory and at http://www.gromacs.org.
9 # GROMACS is free software; you can redistribute it and/or
10 # modify it under the terms of the GNU Lesser General Public License
11 # as published by the Free Software Foundation; either version 2.1
12 # of the License, or (at your option) any later version.
14 # GROMACS is distributed in the hope that it will be useful,
15 # but WITHOUT ANY WARRANTY; without even the implied warranty of
16 # MERCHANTABILITY or FITNESS FOR A PARTICULAR PURPOSE. See the GNU
17 # Lesser General Public License for more details.
19 # You should have received a copy of the GNU Lesser General Public
20 # License along with GROMACS; if not, see
21 # http://www.gnu.org/licenses, or write to the Free Software Foundation,
22 # Inc., 51 Franklin Street, Fifth Floor, Boston, MA 02110-1301 USA.
24 # If you want to redistribute modifications to GROMACS, please
25 # consider that scientific software is very special. Version
26 # control is crucial - bugs must be traceable. We will be happy to
27 # consider code for inclusion in the official distribution, but
28 # derived work must not be called official GROMACS. Details are found
29 # in the README & COPYING files - if they are missing, get the
30 # official version at http://www.gromacs.org.
32 # To help us fund GROMACS development, we humbly ask that you cite
33 # the research papers on the package. Check out http://www.gromacs.org.
35 # OpenCL required version: 1.2 or newer
36 set(REQUIRED_SYCL_MIN_VERSION_MAJOR 1)
37 set(REQUIRED_SYCL_MIN_VERSION_MINOR 2)
38 set(REQUIRED_SYCL_MIN_VERSION ${REQUIRED_SYCL_MIN_VERSION_MAJOR}.${REQUIRED_SYCL_MIN_VERSION_MINOR})
43 message(FATAL_ERROR "SYCL acceleration is not available in double precision")
46 include(gmxFindFlagsForSource)
48 if(CMAKE_CXX_COMPILER MATCHES "dpcpp")
49 # At least Intel dpcpp defaults to having SYCL enabled for all code. This leads to two problems:
51 # 1. Compiles take ~3x longer, since every file has to be compiled for multiple targets.
52 # 2. We get a ton of warnings for the device-specific pass when the compiler sees our SIMD code.
54 # To avoid this, we attempt to find a flag to disable SYCL for non-SYCL files. Unfortunately,
55 # when using gmx_find_flag_for_source() that includes calling check_cxx_compiler_flag(),
56 # this in turn exposes a bug in dpcpp, where an object file compiles with -fno-sycl leads to
57 # a failed link stage (when the same flag is not used). Since none of this is critical, we handle
58 # it by merely checking if it works to compile a source fils with this flag, and choking if SYCL
61 if(NOT CHECK_DISABLE_SYCL_CXX_FLAGS_QUIETLY)
62 message(STATUS "Checking for flags to disable SYCL")
65 gmx_check_source_compiles_with_flags(
66 "int main() { return 0; }"
69 DISABLE_SYCL_CXX_FLAGS_RESULT)
71 if(DISABLE_SYCL_CXX_FLAGS_RESULT)
72 set(DISABLE_SYCL_CXX_FLAGS "-fno-sycl")
74 if(NOT CHECK_DISABLE_SYCL_CXX_FLAGS_QUIETLY)
75 if(DISABLE_SYCL_CXX_FLAGS_RESULT)
76 message(STATUS "Checking for flags to disable SYCL - -fno-sycl")
78 message(WARNING "Cannot find flags to disable SYCL for non-SYCL hardware-specific C++ code. Expect many warnings, but they are likely benign.")
80 set(CHECK_DISABLE_SYCL_CXX_FLAGS_QUIETLY 1 CACHE INTERNAL "Keep quiet on future calls to detect no-SYCL flags" FORCE)
84 # Find the flags to enable (or re-enable) SYCL with Intel extensions. In case we turned it off above,
85 # it's important that we check the combination of both flags, to make sure the second one re-enables SYCL.
86 if(NOT CHECK_SYCL_CXX_FLAGS_QUIETLY)
87 message(STATUS "Checking for flags to enable SYCL")
89 gmx_find_flag_for_source(SYCL_CXX_FLAGS_RESULT
90 "#include <CL/sycl.hpp>
91 namespace sycl = cl::sycl;
93 sycl::queue q(sycl::default_selector{});
96 " "CXX" DISABLE_SYCL_CXX_FLAGS SYCL_CXX_FLAGS "-fsycl -fsycl-device-code-split=per_kernel")
98 if(NOT CHECK_SYCL_CXX_FLAGS_QUIETLY)
99 if(SYCL_CXX_FLAGS_RESULT)
100 message(STATUS "Checking for flags to enable SYCL - ${SYCL_CXX_FLAGS}")
102 set(CHECK_SYCL_CXX_FLAGS_QUIETLY 1 CACHE INTERNAL "Keep quiet on future calls to detect SYCL flags" FORCE)
105 if(NOT SYCL_CXX_FLAGS_RESULT)
106 message(FATAL_ERROR "Cannot compile with SYCL Intel compiler. Try a different compiler or disable SYCL.")
109 # Add function wrapper similar to the one used by ComputeCPP and hipSYCL
110 function(add_sycl_to_target)
111 cmake_parse_arguments(
112 PARSE_ARGV 0 # No positional arguments
113 ARGS # Prefix for the resulting variables
115 "TARGET" # One-value keyword
116 "SOURCES" # Multi-value keyword
118 set_source_files_properties(${ARGS_SOURCES} PROPERTIES COMPILE_FLAGS "${SYCL_CXX_FLAGS}")
119 target_link_libraries(${ARGS_TARGET} PRIVATE ${SYCL_CXX_FLAGS})
120 endfunction(add_sycl_to_target)