1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
32
33
34
35
36
37
38
39
40
41
42
43
44
45
46
47
48
49
50
51
52
53
54
55
56
57
58
59
60
61
62
63
64
65
66
67
68
69
70
71
72
73
74
75
76
77
78
79
80
81
82
83
84
85
86
87
88
89
90
91
92
93
94
95
96
97
98
99
100
101
102
103
104
105
106
107
108
109
110
111
112
113
114
115
116
117
118
119
120
121
122
123
124
125
126
127
128
129
130
131
132
133
134
135
136
137
138
139
140
141
142
143
144
145
146
147
148
149
150
151
152
153
154
155
156
157
158
159
160
161
162
163
164
165
166
167
168
169
170
171
172
173
174
175
176
177
178
179
180
181
182
|
From: Xuanteng Huang <xuanteng.huang@outlook.com>
Date: Wed, 15 May 2024 22:20:47 +0800
Subject: remove assembly code integration
ASM kernel codes are artifacts generated from AMD proprietory sources, which violates DFSG.
Hence we exclude them from source package here.
Forwarded: not-needed
---
src/CMakeLists.txt | 132 -----------------------------------------------------
1 file changed, 132 deletions(-)
diff --git a/src/CMakeLists.txt b/src/CMakeLists.txt
index 95aa501..df1d5ee 100644
--- a/src/CMakeLists.txt
+++ b/src/CMakeLists.txt
@@ -256,92 +256,8 @@ if( MIOPEN_BACKEND MATCHES "OpenCL" OR MIOPEN_BACKEND STREQUAL "HIPOC" OR MIOPEN
set(MIOPEN_KERNEL_INCLUDES
${STATIC_COMPOSABLE_KERNEL_INCLUDE}
${COMPOSABLE_KERNEL_INCLUDE}
- ${COMPOSABLE_KERNEL_DYNAMIC_ASM_INCLUDE}
${GPU_GENERAL_TENSOR_REORDER_KERNEL_HIP_INCLUDE}
include/miopen/implicitgemm_params.hpp
- kernels/Conv_Winograd_v13_3_12_fp16dot_stride1.inc
- kernels/Conv_Winograd_v13_3_12_fp16dot_stride2_dec.inc
- kernels/Conv_Winograd_v13_3_12_fp16dot_stride2_dil.inc
- kernels/Conv_Winograd_v14_3_3_fp16dot_stride1.inc
- kernels/Conv_Winograd_v14_3_3_fp16dot_stride2_dec.inc
- kernels/Conv_Winograd_v14_3_3_fp16dot_stride2_dil.inc
- kernels/Conv_Winograd_v13_3_12_epilogue.inc
- kernels/Conv_Winograd_v13_3_12_prologue.inc
- kernels/Conv_Winograd_v16_5_0_epilogue.inc
- kernels/Conv_Winograd_v16_5_0_prologue.inc
- kernels/Conv_Winograd_v16_5_0_stride1.inc
- kernels/conv_3x3_wheel_alpha_v9_2_7_epilogue.inc
- kernels/conv_3x3_wheel_alpha_v9_2_7_prologue.inc
- kernels/conv_3x3_wheel_alpha_v9_2_7_gfx8_stride_2_dec.inc
- kernels/conv_3x3_wheel_alpha_v9_2_7_gfx8.inc
- kernels/conv_3x3_wheel_alpha_v3_0b_epilogue.inc
- kernels/conv_3x3_wheel_alpha_v3_0b_prologue.inc
- kernels/conv_3x3_wheel_alpha_v3_0b.inc
- kernels/conv_3x3_wheel_alpha_v7_0_3b_epilogue.inc
- kernels/conv_3x3_wheel_alpha_v7_0_3b_prologue.inc
- kernels/conv_3x3_wheel_alpha_v7_0_3b.inc
- kernels/conv_3x3_wheel_alpha_v9_0_15_epilogue.inc
- kernels/conv_3x3_wheel_alpha_v9_0_15_prologue.inc
- kernels/conv_3x3_wheel_alpha_v9_0_15_gfx8_stride_2_dil.inc
- kernels/conv_3x3_wheel_alpha_v9_0_15_gfx8_stride_2_dec.inc
- kernels/conv_3x3_wheel_alpha_v9_0_15_gfx8.inc
- kernels/conv_3x3_wheel_alpha_v9_0_15_gfx9_stride_2_dil.inc
- kernels/conv_3x3_wheel_alpha_v9_0_15_gfx9_stride_2_dec.inc
- kernels/conv_3x3_wheel_alpha_v9_0_15_gfx9.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_f3x2_fp16_dot2_edc_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_f3x2_fp16_dot2_edc_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_f3x2_fp16_dot2_edc_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_f3x2_fp32_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_f3x2_fp32_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_f3x2_fp32_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp16_dot2_edc_dilation2.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp16_dot2_edc_stride1.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp16_dot2_edc_stride2.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp32_dilation2.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp32_stride1.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp32_stride2.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp16_dot2_edc_dilation2.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp16_dot2_edc_stride1.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp16_dot2_edc_stride2.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp32_dilation2.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp32_stride1.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp32_stride2.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp16_dot2_edc_dilation2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp16_dot2_edc_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp16_dot2_edc_stride2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp32_dilation2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp32_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx9_fp32_stride2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp16_dot2_edc_dilation2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp16_dot2_edc_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp16_dot2_edc_stride2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp32_dilation2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp32_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx90a_fp32_stride2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp16_dot2_edc_dilation2.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp16_dot2_edc_stride1.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp16_dot2_edc_stride2.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp32_dilation2.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp32_stride1.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp32_stride2.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp16_dot2_edc_dilation2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp16_dot2_edc_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp16_dot2_edc_stride2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp32_dilation2_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp32_stride1_group.inc
- kernels/Conv_Winograd_v21_1_3_gfx10_fp32_stride2_group.inc
- kernels/Conv_Winograd_v21_1_3_metadata.inc
- kernels/xform_bidirect_winograd_code.inc
- kernels/rocm_version.inc
- kernels/inst_wrappers.inc
- kernels/conv_common.inc
- kernels/utilities.inc
- kernels/xform_data_filter.inc
- kernels/xform_kd_cov2.inc
- kernels/xform_metadata.inc
- kernels/neuron.inc
- kernels/conv_sizes.inc
- kernels/gpr_alloc.inc
kernels/bfloat16_dev.hpp
kernels/float_types.h
kernels/workaround_issue_1431.hpp
@@ -350,10 +266,8 @@ if( MIOPEN_BACKEND MATCHES "OpenCL" OR MIOPEN_BACKEND STREQUAL "HIPOC" OR MIOPEN
set(MIOPEN_KERNELS
${STATIC_COMPOSABLE_KERNEL_SOURCE}
${COMPOSABLE_KERNEL_SOURCE}
- ${COMPOSABLE_KERNEL_DYNAMIC_ASM_SOURCE}
${COMPOSABLE_KERNEL_DYNAMIC_CPP_SOURCE}
${GPU_REFERENCE_KERNEL_HIP}
- ${GPU_REFERENCE_KERNEL_ASM}
${GPU_BATCHED_TRANSPOSE_KERNEL_HIP}
${GPU_GENERAL_TENSOR_REORDER_KERNEL_HIP_SOURCE}
kernels/detect_llvm_amdgcn_buffer_atomic_fadd_f32_float.cpp
@@ -398,61 +312,15 @@ if( MIOPEN_BACKEND MATCHES "OpenCL" OR MIOPEN_BACKEND STREQUAL "HIPOC" OR MIOPEN
kernels/MIOpenConvFwd_LxL_11.cl
kernels/MIOpenConvFFT.cl
kernels/MIOpenRNNHiddenStateUpdate.cl
- kernels/bugzilla_34765_detect.s
- kernels/dummy_kernel.s
- kernels/conv3x3.s
- kernels/conv1x1u.s
- kernels/conv1x1u_stride2.s
- kernels/conv1x1u_bias_activ.s
- kernels/conv3x3wrw.s
- kernels/conv1x1wrw.s
- kernels/conv5x10u2v2f1.s
- kernels/conv5x10u2v2b1.s
- kernels/conv7x7c3h224w224k64u2v2p3q3f1.s
- kernels/xform_out.s
- kernels/gcnAsmBNBwdTrainSpatial.s
kernels/MIOpenTensorKernels.cl
kernels/MIOpenSubTensorOpWithScalarKernel.cl
kernels/MIOpenSubTensorOpWithSubTensorKernel.cl
kernels/MIOpenSubTensorOpWithCastTensorKernel.cl
kernels/MIOpenSubTensorOpWithTransformKernel.cl
- kernels/Conv_Winograd_v13_3_12_fp16dot_stride1.s
- kernels/Conv_Winograd_v13_3_12_fp16dot_stride2_dec.s
- kernels/Conv_Winograd_v13_3_12_fp16dot_stride2_dil.s
- kernels/Conv_Winograd_v14_3_3_fp16dot_stride1.s
- kernels/Conv_Winograd_v14_3_3_fp16dot_stride2_dec.s
- kernels/Conv_Winograd_v14_3_3_fp16dot_stride2_dil.s
- kernels/Conv_Winograd_v16_5_0_stride1.s
- kernels/conv_3x3_wheel_alpha_v9_0_15_stride_2_dil.s
- kernels/conv_3x3_wheel_alpha_v9_0_15_stride_2_dec.s
- kernels/conv_3x3_wheel_alpha_v9_0_15.s
- kernels/conv_3x3_wheel_alpha_v7_0_3b.s
- kernels/conv_3x3_wheel_alpha_v3_0b.s
- kernels/conv_3x3_wheel_alpha_v9_2_7.s
- kernels/conv_3x3_wheel_alpha_v9_2_7_stride_2_dec.s
- kernels/Conv_Winograd_v21_1_3_f3x2_fp16_dot2_edc_stride1_group.s
- kernels/Conv_Winograd_v21_1_3_f3x2_fp32_stride1_group.s
- kernels/Conv_Winograd_v21_1_3_fp16_dot2_edc_dilation2.s
- kernels/Conv_Winograd_v21_1_3_fp16_dot2_edc_stride1.s
- kernels/Conv_Winograd_v21_1_3_fp16_dot2_edc_stride2.s
- kernels/Conv_Winograd_v21_1_3_fp32_dilation2.s
- kernels/Conv_Winograd_v21_1_3_fp32_stride1.s
- kernels/Conv_Winograd_v21_1_3_fp32_stride2.s
- kernels/Conv_Winograd_v21_1_3_fp16_dot2_edc_dilation2_group.s
- kernels/Conv_Winograd_v21_1_3_fp16_dot2_edc_stride1_group.s
- kernels/Conv_Winograd_v21_1_3_fp16_dot2_edc_stride2_group.s
- kernels/Conv_Winograd_v21_1_3_fp32_dilation2_group.s
- kernels/Conv_Winograd_v21_1_3_fp32_stride1_group.s
- kernels/Conv_Winograd_v21_1_3_fp32_stride2_group.s
kernels/MIOpenConvBwdBias.cl
kernels/MIOpenBatchNormActivInfer.cl
kernels/MIOpenCTCLoss.cl
kernels/MIOpenDropout.cl
- kernels/xform_data.s
- kernels/xform_filter.s
- kernels/xform_bidirect_winograd_data.s
- kernels/xform_bidirect_winograd_filter.s
- kernels/xform_bidirect_winograd_out.s
kernels/UniversalTranspose.cl)
# Kernels in development lists.
|
