CMakeLists.txt 11.1 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 "")

Artur Wojcik's avatar
cmakes  
Artur Wojcik committed
115
116
117
set(CMAKE_CXX_STANDARD 17)
set(CMAKE_CXX_STANDARD_REQUIRED ON)
set(CMAKE_CXX_EXTENSIONS OFF)
118

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

Paul's avatar
Paul committed
286
include(ROCMCreatePackage)
Paul Fultz II's avatar
Paul Fultz II committed
287
include(ROCMTest)
Paul's avatar
Paul committed
288

289
290
291
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
292
add_subdirectory(src)
Chris Austen's avatar
Chris Austen committed
293
add_subdirectory(docs)
294
if(BUILD_TESTING)
Paul Fultz II's avatar
Paul Fultz II committed
295
    rocm_enable_test_package(migraphx)
296
297
    add_subdirectory(test)
endif()
Paul's avatar
Paul committed
298
add_subdirectory(tools)
299
300
301
302
303
304
305

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
306
307
308
309

rocm_create_package(
    NAME MIGraphX
    DESCRIPTION "AMD's graph optimizer"
310
    MAINTAINER "AMDMIGraphX Maintainer <migraphx-lib.support@amd.com>"
Chris Austen's avatar
Chris Austen committed
311
312
313
314
    LDCONFIG
    PTH
    DEPENDS miopen-hip rocblas hip-rocclr hip-base half
)