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

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

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