CMakeLists.txt 3.54 KB
Newer Older
Paul's avatar
Paul committed
1
2
3
4

list(APPEND CMAKE_PREFIX_PATH /opt/rocm /opt/rocm/hip /opt/rocm/hcc)
find_package(miopen)

5
6
7
8
# rocblas
find_package(rocblas REQUIRED PATHS /opt/rocm)
message(STATUS "Build with rocblas")

Paul's avatar
Paul committed
9
10
11
12
if(NOT TARGET MIOpen)
    message(SEND_ERROR "Cant find miopen")
endif()

Paul's avatar
Paul committed
13
add_library(migraphx_device
14
    device/acos.cpp
15
    device/acosh.cpp
Paul's avatar
Paul committed
16
    device/add.cpp
17
18
19
20
    device/add_clip.cpp
    device/add_relu.cpp
    device/add_sigmoid.cpp
    device/add_tanh.cpp
Shucai Xiao's avatar
Shucai Xiao committed
21
22
    device/argmax.cpp
    device/argmin.cpp
23
    device/asin.cpp
24
    device/asinh.cpp
25
    device/atan.cpp
26
    device/atanh.cpp
27
28
29
    device/ceil.cpp
    device/clip.cpp
    device/concat.cpp
30
    device/contiguous.cpp
31
    device/convert.cpp
32
33
34
35
36
37
    device/cos.cpp
    device/cosh.cpp
    device/div.cpp
    device/erf.cpp
    device/exp.cpp
    device/floor.cpp
38
    device/gather.cpp
kahmed10's avatar
kahmed10 committed
39
    device/gelu.cpp
40
    device/int8_gemm_pack.cpp
41
42
43
44
45
46
47
48
49
    device/log.cpp
    device/logsoftmax.cpp
    device/max.cpp
    device/min.cpp
    device/mul.cpp
    device/mul_add.cpp
    device/mul_add_relu.cpp
    device/pad.cpp
    device/pow.cpp
Shucai Xiao's avatar
Shucai Xiao committed
50
    device/prelu.cpp
kahmed10's avatar
kahmed10 committed
51
    device/recip.cpp
52
    device/reduce_max.cpp
53
    device/reduce_mean.cpp
Shucai Xiao's avatar
Shucai Xiao committed
54
    device/reduce_min.cpp
55
    device/reduce_sum.cpp
Shucai Xiao's avatar
Shucai Xiao committed
56
    device/reduce_prod.cpp
57
58
59
60
    device/relu.cpp
    device/round.cpp
    device/rsqrt.cpp
    device/sigmoid.cpp
Shucai Xiao's avatar
Shucai Xiao committed
61
    device/sign.cpp
62
63
64
65
66
67
68
69
    device/sin.cpp
    device/sinh.cpp
    device/softmax.cpp
    device/sqdiff.cpp
    device/sqrt.cpp
    device/sub.cpp
    device/tan.cpp
    device/tanh.cpp
70
)
Paul's avatar
Paul committed
71
set_target_properties(migraphx_device PROPERTIES EXPORT_NAME device)
Paul's avatar
Paul committed
72
rocm_set_soversion(migraphx_device ${MIGRAPHX_SO_VERSION})
Paul's avatar
Paul committed
73
rocm_clang_tidy_check(migraphx_device)
Paul Fultz II's avatar
Paul Fultz II committed
74
75
76
77
78
79
80
81
82
target_compile_options(migraphx_device PRIVATE -std=c++17 -fno-gpu-rdc -Wno-unused-command-line-argument)
target_link_libraries(migraphx_device migraphx hip::device -fno-gpu-rdc -Wno-invalid-command-line-argument -Wno-unused-command-line-argument)
if(CMAKE_CXX_COMPILER MATCHES ".*hcc")
    set(AMDGPU_TARGETS "gfx803;gfx900;gfx906" CACHE STRING "")
    foreach(AMDGPU_TARGET ${AMDGPU_TARGETS})
        target_compile_options(migraphx_device PRIVATE -amdgpu-target=${AMDGPU_TARGET})
        target_link_libraries(migraphx_device -amdgpu-target=${AMDGPU_TARGET})
    endforeach()
endif()
Paul's avatar
Paul committed
83
84
target_include_directories(migraphx_device PUBLIC $<BUILD_INTERFACE:${CMAKE_CURRENT_SOURCE_DIR}/include>)
target_include_directories(migraphx_device PRIVATE $<BUILD_INTERFACE:${CMAKE_CURRENT_SOURCE_DIR}/device/include>)
85

Paul's avatar
Paul committed
86
add_library(migraphx_gpu
Shucai Xiao's avatar
Shucai Xiao committed
87
88
    argmax.cpp
    argmin.cpp
89
    eliminate_workspace.cpp
Paul's avatar
Paul committed
90
    fuse_ops.cpp
Paul's avatar
Paul committed
91
    hip.cpp
Paul's avatar
Paul committed
92
    target.cpp
Paul's avatar
Paul committed
93
    lowering.cpp
wsttiger's avatar
wsttiger committed
94
95
    pooling.cpp
    convolution.cpp
kahmed10's avatar
kahmed10 committed
96
    deconvolution.cpp
97
    quant_convolution.cpp
98
    softmax.cpp
99
    logsoftmax.cpp
100
    contiguous.cpp
101
    concat.cpp
Khalique's avatar
Khalique committed
102
    leaky_relu.cpp
103
    batchnorm.cpp
Paul's avatar
Paul committed
104
    write_literals.cpp
105
    rocblas.cpp
Khalique's avatar
Khalique committed
106
    abs.cpp
Khalique's avatar
Khalique committed
107
    elu.cpp
108
    pad.cpp
109
    gather.cpp
Shucai Xiao's avatar
Shucai Xiao committed
110
    convert.cpp
Khalique's avatar
Khalique committed
111
    lrn.cpp
Paul's avatar
Paul committed
112
    schedule_model.cpp
113
    adjust_allocation.cpp
114
    pack_int8_args.cpp
Khalique's avatar
Khalique committed
115
    clip.cpp
116
117
    int8_gemm_pack.cpp
    int8_conv_pack.cpp
118
    gemm_impl.cpp
119
    preallocate_param.cpp
Paul's avatar
Paul committed
120
)
Paul's avatar
Paul committed
121
set_target_properties(migraphx_gpu PROPERTIES EXPORT_NAME gpu)
Paul's avatar
Paul committed
122
rocm_set_soversion(migraphx_gpu ${MIGRAPHX_SO_VERSION})
Paul's avatar
Paul committed
123
rocm_clang_tidy_check(migraphx_gpu)
Paul Fultz II's avatar
Paul Fultz II committed
124
125
# Workaround broken rocblas headers
target_compile_definitions(migraphx_gpu PUBLIC -D__HIP_PLATFORM_HCC__=1)
Paul's avatar
Paul committed
126
127
target_link_libraries(migraphx_gpu PUBLIC migraphx MIOpen roc::rocblas)
target_link_libraries(migraphx_gpu PRIVATE migraphx_device)
mei-ye's avatar
mei-ye committed
128

Paul's avatar
Paul committed
129
rocm_install_targets(
Paul's avatar
Paul committed
130
  TARGETS migraphx_gpu migraphx_device
Paul's avatar
Paul committed
131
132
133
  INCLUDE
    ${CMAKE_CURRENT_SOURCE_DIR}/include
)
mei-ye's avatar
mei-ye committed
134