CMakeLists.txt 11.4 KB
Newer Older
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
#####################################################################################
# The MIT License (MIT)
#
# Copyright (c) 2015-2022 Advanced Micro Devices, Inc. All rights reserved.
#
# Permission is hereby granted, free of charge, to any person obtaining a copy
# of this software and associated documentation files (the "Software"), to deal
# in the Software without restriction, including without limitation the rights
# to use, copy, modify, merge, publish, distribute, sublicense, and/or sell
# copies of the Software, and to permit persons to whom the Software is
# furnished to do so, subject to the following conditions:
#
# The above copyright notice and this permission notice shall be included in
# all copies or substantial portions of the Software.
#
# THE SOFTWARE IS PROVIDED "AS IS", WITHOUT WARRANTY OF ANY KIND, EXPRESS OR
# IMPLIED, INCLUDING BUT NOT LIMITED TO THE WARRANTIES OF MERCHANTABILITY,
# FITNESS FOR A PARTICULAR PURPOSE AND NONINFRINGEMENT.  IN NO EVENT SHALL THE
# AUTHORS OR COPYRIGHT HOLDERS BE LIABLE FOR ANY CLAIM, DAMAGES OR OTHER
# LIABILITY, WHETHER IN AN ACTION OF CONTRACT, TORT OR OTHERWISE, ARISING FROM,
# OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR OTHER DEALINGS IN
# THE SOFTWARE.
#####################################################################################
24
cmake_minimum_required(VERSION 3.15 FATAL_ERROR)
Paul's avatar
Paul committed
25

26
27
28
29
if("${CMAKE_SOURCE_DIR}" STREQUAL "${CMAKE_BINARY_DIR}")
    message(FATAL_ERROR "The binary and source directroy cannot be the same")
endif()

30
# Setup valid strings for build type
31
set(MIGRAPHX_CONFIGURATION_TYPES "Debug;Release;RelWithDebInfo;MinSizeRel")
32

33
get_property(MIGRAPHX_GENERATOR_IS_MULTI_CONFIG GLOBAL PROPERTY GENERATOR_IS_MULTI_CONFIG)
Paul's avatar
Paul committed
34
35
# This has to be initialized before the project() command appears
# Set the default of CMAKE_BUILD_TYPE to be release, unless user specifies with -D.  MSVC_IDE does not use CMAKE_BUILD_TYPE
36
if(NOT MIGRAPHX_GENERATOR_IS_MULTI_CONFIG)
37
38
39
40
41
42
43
44
45
46
    if (NOT CMAKE_BUILD_TYPE)
        set(CMAKE_BUILD_TYPE Release CACHE STRING
            "Choose the type of build, options are: None Debug Release RelWithDebInfo MinSizeRel.")
        set_property(CACHE CMAKE_BUILD_TYPE PROPERTY STRINGS ${MIGRAPHX_CONFIGURATION_TYPES})
    endif()
else()
    if (NOT CMAKE_CONFIGURATION_TYPES)
        set(CMAKE_CONFIGURATION_TYPES ${MIGRAPHX_CONFIGURATION_TYPES} CACHE STRING
                "Available build types (configurations) on multi-config generators")
    endif()
Paul's avatar
Paul committed
47
48
endif()

49
50
51
52
if(NOT WIN32)
    set(CMAKE_INSTALL_PREFIX "/opt/rocm" CACHE PATH "")
    set(CMAKE_BUILD_RPATH "${CMAKE_BINARY_DIR}/lib")
endif()
53

54
list(APPEND CMAKE_PREFIX_PATH /opt/rocm /opt/rocm/llvm $ENV{ROCM_PATH} $ENV{HIP_PATH})
55

56
57
58
project(migraphx LANGUAGES C CXX)
include(CTest)

Paul's avatar
Paul committed
59
find_package(ROCM REQUIRED)
60
find_package(Threads REQUIRED)
turneram's avatar
turneram committed
61

62
63
64
65
66
67
if(WIN32)
option(MIGRAPHX_ENABLE_PYTHON "Enable python bindings" OFF)
else()
option(MIGRAPHX_ENABLE_PYTHON "Enable python bindings" ON)
endif()

68
69
70
# By default build shared libraries
option(BUILD_SHARED_LIBS "Create shared libraries" ON)

Artur Wojcik's avatar
Artur Wojcik committed
71
72
73
74
75
76
if(WIN32) # CK is not yet ported to Windows
option(MIGRAPHX_USE_COMPOSABLEKERNEL "Enable MIGraphX to use composable kernel JIT library" OFF)
else()
option(MIGRAPHX_USE_COMPOSABLEKERNEL "Enable MIGraphX to use composable kernel JIT library" ON)
endif()

turneram's avatar
turneram committed
77
78
79
find_path(HALF_INCLUDE_DIR half.hpp PATH_SUFFIXES half)
if (NOT HALF_INCLUDE_DIR)
    message(FATAL_ERROR "Could not find half.hpp - Please check that the install path of half.hpp has been added to CMAKE_PREFIX_PATH")
80
else()
81
    message(STATUS "half.hpp is at ${HALF_INCLUDE_DIR}")
turneram's avatar
turneram committed
82
83
84
85
86
87
88
89
90
endif()

include(CheckTypeSize)
set(CMAKE_REQUIRED_INCLUDES ${HALF_INCLUDE_DIR})
set(CMAKE_EXTRA_INCLUDE_FILES half.hpp)
check_type_size("half_float::detail::expr" HALF_EXPR LANGUAGE CXX)
set(CMAKE_REQUIRED_INCLUDES)
set(CMAKE_EXTRA_INCLUDE_FILES)

Paul's avatar
Paul committed
91
92
include(ROCMSetupVersion)

93
94
option(BUILD_DEV "Build for development purpose only" OFF)

Umang Yadav's avatar
Umang Yadav committed
95
rocm_setup_version(VERSION 2.9.0)
96
97
math(EXPR MIGRAPHX_SO_MAJOR_VERSION "(${PROJECT_VERSION_MAJOR} * 1000 * 1000) + (${PROJECT_VERSION_MINOR} * 1000) + ${PROJECT_VERSION_PATCH}")
set(MIGRAPHX_SO_VERSION ${MIGRAPHX_SO_MAJOR_VERSION}.0)
Paul's avatar
Paul committed
98

Paul's avatar
Paul committed
99
100
option( BUILD_SHARED_LIBS "Build as a shared library" ON )

101
102
103
include(CheckCXXCompilerFlag)
check_cxx_compiler_flag("--cuda-host-only -x hip" HAS_HIP)
if(HAS_HIP)
104
    message(STATUS "Enable gpu backend")
Paul's avatar
Paul committed
105
    set(MIGRAPHX_ENABLE_GPU On CACHE BOOL "")
Paul's avatar
Paul committed
106
else()
Paul's avatar
Paul committed
107
    set(MIGRAPHX_ENABLE_GPU Off CACHE BOOL "")
Paul's avatar
Paul committed
108
109
endif()

110
111
112
# Disable cpu backend by default
set(MIGRAPHX_ENABLE_CPU Off CACHE BOOL "")

varunsh's avatar
varunsh committed
113
114
115
# Disable fpga backend by default
set(MIGRAPHX_ENABLE_FPGA Off CACHE BOOL "")

116
117
118
119
if(WIN32)
    add_compile_definitions("$<$<COMPILE_LANGUAGE:C,CXX>:_CRT_SECURE_NO_WARNINGS;_USE_MATH_DEFINES>")
endif()

120
set(CMAKE_CXX_STANDARD_DEFAULT "")
121
122
123
124
125
if(MSVC)
    add_compile_options($<$<COMPILE_LANGUAGE:CXX>:/std:c++17>)
else()
    add_compile_options($<$<COMPILE_LANGUAGE:CXX>:-std=c++17>)
endif()
126

Paul's avatar
Paul committed
127
128
list(APPEND CMAKE_MODULE_PATH ${CMAKE_CURRENT_SOURCE_DIR}/cmake)
include(EnableCompilerWarnings)
Paul's avatar
Paul committed
129
include(ROCMClangTidy)
130
if(CMAKE_CXX_COMPILER MATCHES ".*clang\\+\\+.*")
Paul's avatar
Paul committed
131
132
133
134
135
    set(MIGRAPHX_TIDY_ERRORS ERRORS * -readability-inconsistent-declaration-parameter-name)
# Enable tidy on hip
elseif(MIGRAPHX_ENABLE_GPU)
    set(MIGRAPHX_TIDY_ERRORS ALL)
endif()
Paul's avatar
Paul committed
136
137
rocm_enable_clang_tidy(
    CHECKS
138
139
140
141
142
143
144
145
146
147
148
        boost-*
        bugprone-*
        cert-*
        clang-analyzer-*
        clang-diagnostic-*
        cppcoreguidelines-*
        google-*
        hicpp-multiway-paths-covered
        hicpp-signed-bitwise
        llvm-namespace-comment
        misc-*
149
	-misc-confusable-identifiers
150
        -misc-use-anonymous-namespace
151
152
153
        modernize-*
        performance-*
        readability-*
154
155
        -bugprone-easily-swappable-parameters
        -bugprone-implicit-widening-of-multiplication-result
Paul Fultz II's avatar
Paul Fultz II committed
156
        -bugprone-macro-parentheses
157
        -bugprone-signed-char-misuse
158
        -bugprone-unchecked-optional-access
159
160
161
        # Disable the aliased reserved identifiers
        -cert-dcl37-c
        -cert-dcl51-cpp
162
        -cert-err33-c
163
        -cert-str34-c
Paul's avatar
Paul committed
164
165
166
167
168
169
170
171
172
173
174
175
176
        # Disable all alpha checks by default
        -clang-analyzer-alpha*
        # Enable some alpha checks
        clang-analyzer-alpha.core.CallAndMessageUnInitRefArg
        clang-analyzer-alpha.core.Conversion
        clang-analyzer-alpha.core.IdenticalExpr
        clang-analyzer-alpha.core.PointerArithm
        clang-analyzer-alpha.core.PointerSub
        clang-analyzer-alpha.core.TestAfterDivZero
        clang-analyzer-alpha.cplusplus.InvalidIterator
        clang-analyzer-alpha.cplusplus.IteratorRange
        clang-analyzer-alpha.cplusplus.MismatchedIterator
        clang-analyzer-alpha.cplusplus.MisusedMovedObject
Paul's avatar
Paul committed
177
178
179
        -clang-analyzer-optin.performance.Padding
        -clang-diagnostic-deprecated-declarations
        -clang-diagnostic-extern-c-compat
Paul's avatar
Paul committed
180
        -clang-diagnostic-disabled-macro-expansion
Paul's avatar
Paul committed
181
        -clang-diagnostic-unused-command-line-argument
182
183
        -cppcoreguidelines-avoid-do-while
        -cppcoreguidelines-avoid-const-or-ref-data-members
Paul's avatar
Paul committed
184
        -cppcoreguidelines-explicit-virtual-functions
Paul Fultz II's avatar
Paul Fultz II committed
185
        -cppcoreguidelines-init-variables
Paul's avatar
Paul committed
186
187
188
189
190
191
192
193
        -cppcoreguidelines-pro-bounds-array-to-pointer-decay
        -cppcoreguidelines-pro-bounds-constant-array-index
        -cppcoreguidelines-pro-bounds-pointer-arithmetic
        -cppcoreguidelines-pro-type-member-init
        -cppcoreguidelines-pro-type-reinterpret-cast
        -cppcoreguidelines-pro-type-union-access
        -cppcoreguidelines-pro-type-vararg
        -cppcoreguidelines-special-member-functions
194
        -cppcoreguidelines-virtual-class-destructor
195
196
        -cppcoreguidelines-avoid-capture-default-when-capturing-this
        -cppcoreguidelines-rvalue-reference-param-not-moved
197
        -google-readability-*
Paul's avatar
Paul committed
198
199
        -google-runtime-int
        -google-runtime-references
Paul's avatar
Paul committed
200
        -misc-macro-parentheses
201
        -misc-no-recursion
202
        -modernize-concat-nested-namespaces
Paul's avatar
Paul committed
203
204
        -modernize-pass-by-value
        -modernize-use-default-member-init
205
206
        -modernize-use-nodiscard
        -modernize-use-override
Paul's avatar
Paul committed
207
        -modernize-use-trailing-return-type
Paul's avatar
Paul committed
208
        -modernize-use-transparent-functors
Paul's avatar
Paul committed
209
        -performance-type-promotion-in-math-fn
Paul's avatar
Paul committed
210
        -readability-braces-around-statements
Paul Fultz II's avatar
Paul Fultz II committed
211
        -readability-convert-member-functions-to-static
Paul's avatar
Paul committed
212
        -readability-else-after-return
213
        -readability-function-cognitive-complexity
214
        -readability-identifier-length
Paul's avatar
Paul committed
215
        -readability-named-parameter
216
        -readability-redundant-string-init
217
        -readability-suspicious-call-argument
218
        -readability-uppercase-literal-suffix
Paul's avatar
Paul committed
219
        -*-avoid-c-arrays
Paul's avatar
Paul committed
220
        -*-explicit-constructor
Paul's avatar
Paul committed
221
        -*-magic-numbers
Paul Fultz II's avatar
Paul Fultz II committed
222
        -*-narrowing-conversions
Paul's avatar
Paul committed
223
224
        -*-non-private-member-variables-in-classes
        -*-use-auto
Paul's avatar
Paul committed
225
226
        -*-use-emplace
        -*-use-equals-default
Paul's avatar
Paul committed
227
    ${MIGRAPHX_TIDY_ERRORS}
Paul's avatar
Paul committed
228
229
230
    HEADER_FILTER
        ".*hpp"
    EXTRA_ARGS
kahmed10's avatar
kahmed10 committed
231
        -UNDEBUG
Paul's avatar
Paul committed
232
        -DMIGRAPHX_USE_CLANG_TIDY
Paul's avatar
Paul committed
233
234
235
236
237
238
239
240
    CLANG_ARGS
        -analyzer-max-loop 10
        -analyzer-inline-max-stack-depth 10
        -analyzer-config optin.cplusplus.UninitializedObject:Pedantic=true
        -analyzer-config widen-loops=true
        -analyzer-config unroll-loops=true
        -analyzer-config cfg-lifetime=true
        -analyzer-config cfg-scopes=true
Paul's avatar
Paul committed
241
242
243
)
include(ROCMCppCheck)
rocm_enable_cppcheck(
Paul's avatar
Paul committed
244
    CHECKS
Paul's avatar
Paul committed
245
246
247
248
        warning
        style
        performance
        portability
249
    SUPPRESS
Paul's avatar
Paul committed
250
251
252
        ConfigurationNotChecked
        unmatchedSuppression
        unusedFunction
253
        ctuPointerArith
Paul's avatar
Paul committed
254
255
256
        noExplicitConstructor
        passedByValue
        unusedStructMember
Paul's avatar
Paul committed
257
        functionStatic
258
        functionConst
Paul's avatar
Paul committed
259
260
        shadowFunction
        shadowVar
Paul's avatar
Paul committed
261
262
        shadowVariable
        unsafeClassDivZero
263
264
        # Disable because of too many FPs
        arithOperationsOnVoidPointer
Paul's avatar
Paul committed
265
        definePrefix:*test/include/test.hpp
266
        ctuOneDefinitionRuleViolation:*test/*
Paul's avatar
Paul committed
267
268
        useSmartPointer:*src/api/api.cpp
        useSmartPointer:*make_shared_array.hpp
Paul's avatar
Paul committed
269
    FORCE
Paul's avatar
Paul committed
270
    INCONCLUSIVE
Paul's avatar
Paul committed
271
272
    RULE_FILE
        ${CMAKE_CURRENT_SOURCE_DIR}/cppcheck.rules
Paul's avatar
Paul committed
273
    SOURCES
274
        examples/
Paul's avatar
Paul committed
275
276
277
        src/
        test/
    INCLUDE
Paul's avatar
Paul committed
278
279
        ${CMAKE_CURRENT_SOURCE_DIR}/src/include
        ${CMAKE_CURRENT_SOURCE_DIR}/src/targets/cpu/include
Paul's avatar
Paul committed
280
281
282
        ${CMAKE_CURRENT_SOURCE_DIR}/src/targets/gpu/include
        ${CMAKE_CURRENT_SOURCE_DIR}/src/targets/gpu/device/include
        ${CMAKE_CURRENT_SOURCE_DIR}/src/targets/gpu/kernels/include
Paul's avatar
Paul committed
283
        ${CMAKE_CURRENT_SOURCE_DIR}/test/include
Paul's avatar
Paul committed
284
    DEFINE
285
        MIGRAPHX_MLIR=1
Paul's avatar
Paul committed
286
        CPPCHECK=1
Paul's avatar
Paul committed
287
288
        __device__=
        __host__=
Paul Fultz II's avatar
Paul Fultz II committed
289
        __global__=
290
291
    UNDEFINE
        MIGRAPHX_USE_CLANG_TIDY
Paul's avatar
Paul committed
292
)
Paul's avatar
Paul committed
293

Paul's avatar
Paul committed
294
include(ROCMCreatePackage)
Paul Fultz II's avatar
Paul Fultz II committed
295
include(ROCMTest)
Paul's avatar
Paul committed
296

297
298
299
set(CMAKE_LIBRARY_OUTPUT_DIRECTORY ${CMAKE_CURRENT_BINARY_DIR}/lib)
set(CMAKE_ARCHIVE_OUTPUT_DIRECTORY ${CMAKE_CURRENT_BINARY_DIR}/lib)
set(CMAKE_RUNTIME_OUTPUT_DIRECTORY ${CMAKE_CURRENT_BINARY_DIR}/bin)
Paul's avatar
Paul committed
300
add_subdirectory(src)
Chris Austen's avatar
Chris Austen committed
301
add_subdirectory(docs)
302
if(BUILD_TESTING)
Paul Fultz II's avatar
Paul Fultz II committed
303
    rocm_enable_test_package(migraphx)
304
305
    add_subdirectory(test)
endif()
Paul's avatar
Paul committed
306
add_subdirectory(tools)
307
308
309
310
311
312
313

set(DEST_DIR ${CMAKE_BINARY_DIR})
file(GLOB backend_files ${CMAKE_SOURCE_DIR}/src/py/backend/*.py)
file(MAKE_DIRECTORY ${DEST_DIR}/lib/onnx_migraphx)
foreach(py_file ${backend_files})
    configure_file(${py_file} ${DEST_DIR}/lib/onnx_migraphx/. COPYONLY)
endforeach(py_file)
Chris Austen's avatar
Chris Austen committed
314
315
316
317

rocm_create_package(
    NAME MIGraphX
    DESCRIPTION "AMD's graph optimizer"
318
    MAINTAINER "AMDMIGraphX Maintainer <migraphx-lib.support@amd.com>"
Chris Austen's avatar
Chris Austen committed
319
320
321
322
    LDCONFIG
    PTH
    DEPENDS miopen-hip rocblas hip-rocclr hip-base half
)