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
set(CMAKE_INSTALL_PREFIX "/opt/rocm" CACHE PATH "")

46
47
set(CMAKE_BUILD_RPATH "${CMAKE_BINARY_DIR}/lib")

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

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

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

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()

Artur Wojcik's avatar
Artur Wojcik committed
62
63
64
65
66
67
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
Artur Wojcik committed
68
69
70
# By default build shared libraries
option(BUILD_SHARED_LIBS "Create shared libraries" ON)

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

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

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

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

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

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

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

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

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

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

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

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

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

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