CMakeLists.txt 3.5 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
39
    device/int8_gemm_pack.cpp
40
41
42
43
44
45
46
47
48
    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
49
    device/prelu.cpp
50
    device/reduce_max.cpp
51
    device/reduce_mean.cpp
Shucai Xiao's avatar
Shucai Xiao committed
52
    device/reduce_min.cpp
53
    device/reduce_sum.cpp
Shucai Xiao's avatar
Shucai Xiao committed
54
    device/reduce_prod.cpp
55
56
57
58
    device/relu.cpp
    device/round.cpp
    device/rsqrt.cpp
    device/sigmoid.cpp
Shucai Xiao's avatar
Shucai Xiao committed
59
    device/sign.cpp
60
61
62
63
64
65
66
67
    device/sin.cpp
    device/sinh.cpp
    device/softmax.cpp
    device/sqdiff.cpp
    device/sqrt.cpp
    device/sub.cpp
    device/tan.cpp
    device/tanh.cpp
68
)
Paul's avatar
Paul committed
69
set_target_properties(migraphx_device PROPERTIES EXPORT_NAME device)
Paul's avatar
Paul committed
70
rocm_set_soversion(migraphx_device ${MIGRAPHX_SO_VERSION})
Paul's avatar
Paul committed
71
rocm_clang_tidy_check(migraphx_device)
Paul Fultz II's avatar
Paul Fultz II committed
72
73
74
75
76
77
78
79
80
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
81
82
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>)
83

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

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