CMakeLists.txt 11.3 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
31
32
33
# Setup valid strings for build type
if (NOT CMAKE_CONFIGURATION_TYPES)
    set(CMAKE_CONFIGURATION_TYPES "Debug;Release;RelWithDebInfo;MinSizeRel" CACHE STRING "Configs")
endif()
34

35
get_property(MIGRAPHX_GENERATOR_IS_MULTI_CONFIG GLOBAL PROPERTY GENERATOR_IS_MULTI_CONFIG)
Paul's avatar
Paul committed
36
37
# 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
38
39
40
41
if(NOT MIGRAPHX_GENERATOR_IS_MULTI_CONFIG)
    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 ${CMAKE_CONFIGURATION_TYPES})
Paul's avatar
Paul committed
42
43
endif()

44
45
46
47
if(NOT WIN32)
    set(CMAKE_INSTALL_PREFIX "/opt/rocm" CACHE PATH "")
    set(CMAKE_BUILD_RPATH "${CMAKE_BINARY_DIR}/lib")
endif()
48

Artur Wojcik's avatar
cmakes  
Artur Wojcik committed
49
50
list(APPEND CMAKE_PREFIX_PATH /opt/rocm /opt/rocm/llvm $ENV{ROCM_PATH} $ENV{HIP_PATH})

51
52
53
project(migraphx LANGUAGES C CXX)
include(CTest)

Paul's avatar
Paul committed
54
find_package(ROCM REQUIRED)
55
find_package(Threads REQUIRED)
turneram's avatar
turneram committed
56

57
58
59
60
61
if(WIN32)
option(MIGRAPHX_ENABLE_PYTHON "Enable python bindings" OFF)
else()
option(MIGRAPHX_ENABLE_PYTHON "Enable python bindings" ON)
endif()
62

63
64
65
# By default build shared libraries
option(BUILD_SHARED_LIBS "Create shared libraries" ON)

Artur Wojcik's avatar
Artur Wojcik committed
66
67
68
69
70
71
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()

Artur Wojcik's avatar
cmakes  
Artur Wojcik committed
72
73
74
if(WIN32)
    add_compile_definitions($<$<COMPILE_LANGUAGE:C,CXX>:_CRT_SECURE_NO_WARNINGS>)
    add_subdirectory(extern)
75
else()
Artur Wojcik's avatar
cmakes  
Artur Wojcik committed
76
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")
    endif()
turneram's avatar
turneram committed
80
endif()
Artur Wojcik's avatar
cmakes  
Artur Wojcik committed
81
message(STATUS "half.hpp is at ${HALF_INCLUDE_DIR}")
turneram's avatar
turneram committed
82
83
84
85
86
87
88
89

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
90
91
include(ROCMSetupVersion)

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

Umang Yadav's avatar
Umang Yadav committed
94
rocm_setup_version(VERSION 2.9.0)
95
96
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
97

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

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

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

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

115
if(WIN32)
Artur Wojcik's avatar
Artur Wojcik committed
116
    add_compile_definitions("$<$<COMPILE_LANGUAGE:C,CXX>:_CRT_SECURE_NO_WARNINGS;_USE_MATH_DEFINES>")
117
118
endif()

Artur Wojcik's avatar
Artur Wojcik committed
119
set(CMAKE_CXX_STANDARD_DEFAULT "")
120
121
122
123
124
if(MSVC)
    add_compile_options($<$<COMPILE_LANGUAGE:CXX>:/std:c++17>)
else()
    add_compile_options($<$<COMPILE_LANGUAGE:CXX>:-std=c++17>)
endif()
125

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

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

296
297
298
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
299
add_subdirectory(src)
Chris Austen's avatar
Chris Austen committed
300
add_subdirectory(docs)
301
if(BUILD_TESTING)
Paul Fultz II's avatar
Paul Fultz II committed
302
    rocm_enable_test_package(migraphx)
303
304
    add_subdirectory(test)
endif()
Paul's avatar
Paul committed
305
add_subdirectory(tools)
306
307
308
309
310
311
312

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
313
314
315
316

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