CMakeLists.txt 3.6 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
Shucai Xiao's avatar
Shucai Xiao committed
70
    device/rnn_variable_seq_lens.cpp
71
)
Paul's avatar
Paul committed
72
set_target_properties(migraphx_device PROPERTIES EXPORT_NAME device)
Paul's avatar
Paul committed
73
rocm_set_soversion(migraphx_device ${MIGRAPHX_SO_VERSION})
Paul's avatar
Paul committed
74
rocm_clang_tidy_check(migraphx_device)
Paul Fultz II's avatar
Paul Fultz II committed
75
76
77
78
79
80
81
82
83
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
84
85
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>)
86

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

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