1 |
commit: 8e5f37aba0dbc39c1e7ebf2b439d3b9b177821e1 |
2 |
Author: Yiyang Wu <xgreenlandforwyy <AT> gmail <DOT> com> |
3 |
AuthorDate: Thu Sep 22 03:32:03 2022 +0000 |
4 |
Commit: Andrew Ammerlaan <andrewammerlaan <AT> gentoo <DOT> org> |
5 |
CommitDate: Thu Sep 22 10:18:40 2022 +0000 |
6 |
URL: https://gitweb.gentoo.org/repo/gentoo.git/commit/?id=8e5f37ab |
7 |
|
8 |
sci-libs/miopen: shrink 5.1.3-gfx1031.patch to fix QA warning |
9 |
|
10 |
Signed-off-by: Yiyang Wu <xgreenlandforwyy <AT> gmail.com> |
11 |
Signed-off-by: Andrew Ammerlaan <andrewammerlaan <AT> gentoo.org> |
12 |
|
13 |
sci-libs/miopen/files/miopen-5.1.3-gfx1031.patch | 22 ---------------------- |
14 |
1 file changed, 22 deletions(-) |
15 |
|
16 |
diff --git a/sci-libs/miopen/files/miopen-5.1.3-gfx1031.patch b/sci-libs/miopen/files/miopen-5.1.3-gfx1031.patch |
17 |
index 42041f2414ed..de22d66d887a 100644 |
18 |
--- a/sci-libs/miopen/files/miopen-5.1.3-gfx1031.patch |
19 |
+++ b/sci-libs/miopen/files/miopen-5.1.3-gfx1031.patch |
20 |
@@ -14,7 +14,6 @@ Enable gfx1031 support |
21 |
{ |
22 |
assert(num_cu == 110); |
23 |
Only in MIOpen-rocm-5.1.3: patches |
24 |
-diff --color -upr MIOpen-rocm-5.1.3/src/composable_kernel/composable_kernel/include/utility/config.hpp gfx1031/src/composable_kernel/composable_kernel/include/utility/config.hpp |
25 |
--- MIOpen-rocm-5.1.3/src/composable_kernel/composable_kernel/include/utility/config.hpp 2022-05-08 14:08:05.000000000 +0800 |
26 |
+++ gfx1031/src/composable_kernel/composable_kernel/include/utility/config.hpp 2022-09-01 18:36:18.634980274 +0800 |
27 |
@@ -13,7 +13,7 @@ |
28 |
@@ -44,7 +43,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/composable_kernel/composable_kernel/incl |
29 |
#define CK_USE_AMD_V_FMAC_F32 |
30 |
#define CK_USE_AMD_V_DOT2_F32_F16 |
31 |
#define CK_USE_AMD_V_DOT4_I32_I8 |
32 |
-diff --color -upr MIOpen-rocm-5.1.3/src/include/miopen/solver/ck_utility_common.hpp gfx1031/src/include/miopen/solver/ck_utility_common.hpp |
33 |
--- MIOpen-rocm-5.1.3/src/include/miopen/solver/ck_utility_common.hpp 2022-05-08 14:08:05.000000000 +0800 |
34 |
+++ gfx1031/src/include/miopen/solver/ck_utility_common.hpp 2022-09-01 18:36:18.638980266 +0800 |
35 |
@@ -54,6 +54,7 @@ static inline bool is_ck_supported_hardw |
36 |
@@ -64,7 +62,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/include/miopen/solver/ck_utility_common. |
37 |
|
38 |
// buffer atomic-fadd |
39 |
compiler_flag << " -DCK_USE_AMD_BUFFER_ATOMIC_FADD=" |
40 |
-diff --color -upr MIOpen-rocm-5.1.3/src/include/miopen/solver/implicitgemm_util.hpp gfx1031/src/include/miopen/solver/implicitgemm_util.hpp |
41 |
--- MIOpen-rocm-5.1.3/src/include/miopen/solver/implicitgemm_util.hpp 2022-05-08 14:08:05.000000000 +0800 |
42 |
+++ gfx1031/src/include/miopen/solver/implicitgemm_util.hpp 2022-09-01 18:36:18.638980266 +0800 |
43 |
@@ -469,7 +469,7 @@ static inline bool is_use_amd_buffer_loa |
44 |
@@ -95,7 +92,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/include/miopen/solver/implicitgemm_util. |
45 |
} |
46 |
|
47 |
// greatest common divisor, aka highest common factor |
48 |
-diff --color -upr MIOpen-rocm-5.1.3/src/kernels/batchnorm_functions.h gfx1031/src/kernels/batchnorm_functions.h |
49 |
--- MIOpen-rocm-5.1.3/src/kernels/batchnorm_functions.h 2022-05-08 14:08:05.000000000 +0800 |
50 |
+++ gfx1031/src/kernels/batchnorm_functions.h 2022-09-01 18:36:18.858979772 +0800 |
51 |
@@ -159,6 +159,10 @@ |
52 |
@@ -109,7 +105,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/kernels/batchnorm_functions.h gfx1031/sr |
53 |
#define UNUSED __attribute__((__unused__)) |
54 |
|
55 |
#if(MIO_BN_VARIANT != 4) |
56 |
-diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivBwdPerAct.cl gfx1031/src/kernels/MIOpenBatchNormActivBwdPerAct.cl |
57 |
--- MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivBwdPerAct.cl 2022-05-08 14:08:05.000000000 +0800 |
58 |
+++ gfx1031/src/kernels/MIOpenBatchNormActivBwdPerAct.cl 2022-09-01 18:36:18.858979772 +0800 |
59 |
@@ -34,7 +34,7 @@ |
60 |
@@ -121,7 +116,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivBwdPerAct.cl |
61 |
#undef MIOPEN_USE_AMDGCN |
62 |
#define MIOPEN_USE_AMDGCN 1 |
63 |
#endif |
64 |
-diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivBwdSpatial.cl gfx1031/src/kernels/MIOpenBatchNormActivBwdSpatial.cl |
65 |
--- MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivBwdSpatial.cl 2022-05-08 14:08:05.000000000 +0800 |
66 |
+++ gfx1031/src/kernels/MIOpenBatchNormActivBwdSpatial.cl 2022-09-01 18:36:18.858979772 +0800 |
67 |
@@ -32,7 +32,7 @@ |
68 |
@@ -133,7 +127,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivBwdSpatial.c |
69 |
#undef MIOPEN_USE_AMDGCN |
70 |
#define MIOPEN_USE_AMDGCN 1 |
71 |
#endif |
72 |
-diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivFwdTrainSpatial.cl gfx1031/src/kernels/MIOpenBatchNormActivFwdTrainSpatial.cl |
73 |
--- MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivFwdTrainSpatial.cl 2022-05-08 14:08:05.000000000 +0800 |
74 |
+++ gfx1031/src/kernels/MIOpenBatchNormActivFwdTrainSpatial.cl 2022-09-01 18:36:18.858979772 +0800 |
75 |
@@ -33,7 +33,7 @@ |
76 |
@@ -145,7 +138,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormActivFwdTrainSpat |
77 |
#undef MIOPEN_USE_AMDGCN |
78 |
#define MIOPEN_USE_AMDGCN 1 |
79 |
#endif |
80 |
-diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormBwdSpatial.cl gfx1031/src/kernels/MIOpenBatchNormBwdSpatial.cl |
81 |
--- MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormBwdSpatial.cl 2022-05-08 14:08:05.000000000 +0800 |
82 |
+++ gfx1031/src/kernels/MIOpenBatchNormBwdSpatial.cl 2022-09-01 18:36:18.858979772 +0800 |
83 |
@@ -33,7 +33,7 @@ |
84 |
@@ -157,7 +149,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormBwdSpatial.cl gfx |
85 |
#undef MIOPEN_USE_AMDGCN |
86 |
#define MIOPEN_USE_AMDGCN 1 |
87 |
#endif |
88 |
-diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormFwdTrainSpatial.cl gfx1031/src/kernels/MIOpenBatchNormFwdTrainSpatial.cl |
89 |
--- MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormFwdTrainSpatial.cl 2022-05-08 14:08:05.000000000 +0800 |
90 |
+++ gfx1031/src/kernels/MIOpenBatchNormFwdTrainSpatial.cl 2022-09-01 18:36:18.858979772 +0800 |
91 |
@@ -33,7 +33,7 @@ |
92 |
@@ -169,7 +160,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/kernels/MIOpenBatchNormFwdTrainSpatial.c |
93 |
#undef MIOPEN_USE_AMDGCN |
94 |
#define MIOPEN_USE_AMDGCN 1 |
95 |
#endif |
96 |
-diff --color -upr MIOpen-rocm-5.1.3/src/md_graph.cpp gfx1031/src/md_graph.cpp |
97 |
--- MIOpen-rocm-5.1.3/src/md_graph.cpp 2022-05-08 14:08:05.000000000 +0800 |
98 |
+++ gfx1031/src/md_graph.cpp 2022-09-01 18:36:18.630980283 +0800 |
99 |
@@ -738,8 +738,8 @@ void FusionMDGraph::InitConv(FusionMDGra |
100 |
@@ -183,7 +173,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/md_graph.cpp gfx1031/src/md_graph.cpp |
101 |
} |
102 |
} |
103 |
|
104 |
-diff --color -upr MIOpen-rocm-5.1.3/src/ocl/fusionopbiasbnactivocl.cpp gfx1031/src/ocl/fusionopbiasbnactivocl.cpp |
105 |
--- MIOpen-rocm-5.1.3/src/ocl/fusionopbiasbnactivocl.cpp 2022-05-08 14:08:05.000000000 +0800 |
106 |
+++ gfx1031/src/ocl/fusionopbiasbnactivocl.cpp 2022-09-01 18:36:18.634980274 +0800 |
107 |
@@ -392,7 +392,8 @@ miopenStatus_t BatchNormBwdTrainFusionOp |
108 |
@@ -206,7 +195,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/ocl/fusionopbiasbnactivocl.cpp gfx1031/s |
109 |
|
110 |
compile_config += add; |
111 |
MIOPEN_LOG_I2(add); |
112 |
-diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_per_activation.cpp gfx1031/src/solver/batchnorm/backward_per_activation.cpp |
113 |
--- MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_per_activation.cpp 2022-05-08 14:08:05.000000000 +0800 |
114 |
+++ gfx1031/src/solver/batchnorm/backward_per_activation.cpp 2022-09-01 18:36:18.638980266 +0800 |
115 |
@@ -113,6 +113,7 @@ BnBwdTrainingPerActivation::GetSolution( |
116 |
@@ -217,7 +205,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_per_activation |
117 |
}; |
118 |
|
119 |
kernel.comp_options = build_params.GenerateFor(kbp::OpenCL{}); |
120 |
-diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_spatial_multiple.cpp gfx1031/src/solver/batchnorm/backward_spatial_multiple.cpp |
121 |
--- MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_spatial_multiple.cpp 2022-05-08 14:08:05.000000000 +0800 |
122 |
+++ gfx1031/src/solver/batchnorm/backward_spatial_multiple.cpp 2022-09-01 18:36:18.638980266 +0800 |
123 |
@@ -210,6 +210,7 @@ ConvSolution BnBwdTrainingSpatialMultipl |
124 |
@@ -228,7 +215,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_spatial_multip |
125 |
{"MIO_LAYOUT_NHWC", static_cast<int>(problem.IsLayoutNHWC())}, |
126 |
}; |
127 |
|
128 |
-diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_spatial_single.cpp gfx1031/src/solver/batchnorm/backward_spatial_single.cpp |
129 |
--- MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_spatial_single.cpp 2022-05-08 14:08:05.000000000 +0800 |
130 |
+++ gfx1031/src/solver/batchnorm/backward_spatial_single.cpp 2022-09-01 18:36:18.638980266 +0800 |
131 |
@@ -247,6 +247,7 @@ BnBwdTrainingSpatialSingle::GetSolution( |
132 |
@@ -239,7 +225,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/backward_spatial_single |
133 |
}; |
134 |
|
135 |
kernel.comp_options = build_params.GenerateFor(kbp::OpenCL{}); |
136 |
-diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_inference.cpp gfx1031/src/solver/batchnorm/forward_inference.cpp |
137 |
--- MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_inference.cpp 2022-05-08 14:08:05.000000000 +0800 |
138 |
+++ gfx1031/src/solver/batchnorm/forward_inference.cpp 2022-09-01 18:36:18.638980266 +0800 |
139 |
@@ -103,6 +103,7 @@ ConvSolution BnFwdInference::GetSolution |
140 |
@@ -250,7 +235,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_inference.cpp g |
141 |
}; |
142 |
|
143 |
kernel.comp_options = build_params.GenerateFor(kbp::OpenCL{}); |
144 |
-diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_per_activation.cpp gfx1031/src/solver/batchnorm/forward_per_activation.cpp |
145 |
--- MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_per_activation.cpp 2022-05-08 14:08:05.000000000 +0800 |
146 |
+++ gfx1031/src/solver/batchnorm/forward_per_activation.cpp 2022-09-01 18:36:18.638980266 +0800 |
147 |
@@ -105,6 +105,7 @@ BnFwdTrainingPerActivation::GetSolution( |
148 |
@@ -261,7 +245,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_per_activation. |
149 |
}; |
150 |
|
151 |
auto kernel = KernelInfo{}; |
152 |
-diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_spatial_multiple.cpp gfx1031/src/solver/batchnorm/forward_spatial_multiple.cpp |
153 |
--- MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_spatial_multiple.cpp 2022-05-08 14:08:05.000000000 +0800 |
154 |
+++ gfx1031/src/solver/batchnorm/forward_spatial_multiple.cpp 2022-09-01 18:36:18.638980266 +0800 |
155 |
@@ -177,6 +177,7 @@ ConvSolution BnFwdTrainingSpatialMultipl |
156 |
@@ -272,7 +255,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_spatial_multipl |
157 |
{"MIO_LAYOUT_NHWC", static_cast<int>(problem.IsLayoutNHWC())}, |
158 |
}; |
159 |
|
160 |
-diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_spatial_single.cpp gfx1031/src/solver/batchnorm/forward_spatial_single.cpp |
161 |
--- MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_spatial_single.cpp 2022-05-08 14:08:05.000000000 +0800 |
162 |
+++ gfx1031/src/solver/batchnorm/forward_spatial_single.cpp 2022-09-01 18:36:18.638980266 +0800 |
163 |
@@ -211,6 +211,7 @@ BnFwdTrainingSpatialSingle::GetSolution( |
164 |
@@ -283,7 +265,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/solver/batchnorm/forward_spatial_single. |
165 |
{"MIO_LAYOUT_NHWC", static_cast<int>(problem.IsLayoutNHWC())}, |
166 |
}; |
167 |
|
168 |
-diff --color -upr MIOpen-rocm-5.1.3/src/target_properties.cpp gfx1031/src/target_properties.cpp |
169 |
--- MIOpen-rocm-5.1.3/src/target_properties.cpp 2022-05-08 14:08:05.000000000 +0800 |
170 |
+++ gfx1031/src/target_properties.cpp 2022-09-01 18:36:18.630980283 +0800 |
171 |
@@ -54,6 +54,7 @@ static std::string GetDeviceNameFromMap( |
172 |
@@ -294,7 +275,6 @@ diff --color -upr MIOpen-rocm-5.1.3/src/target_properties.cpp gfx1031/src/target |
173 |
}; |
174 |
|
175 |
const char* const p_asciz = miopen::GetStringEnv(MIOPEN_DEBUG_ENFORCE_DEVICE{}); |
176 |
-diff --color -upr MIOpen-rocm-5.1.3/test/CMakeLists.txt gfx1031/test/CMakeLists.txt |
177 |
--- MIOpen-rocm-5.1.3/test/CMakeLists.txt 2022-05-08 14:08:05.000000000 +0800 |
178 |
+++ gfx1031/test/CMakeLists.txt 2022-09-01 18:36:19.022979405 +0800 |
179 |
@@ -38,6 +38,7 @@ option( MIOPEN_TEST_GFX90A "Test on gfx9 |
180 |
@@ -371,7 +351,6 @@ diff --color -upr MIOpen-rocm-5.1.3/test/CMakeLists.txt gfx1031/test/CMakeLists. |
181 |
AND is_full_check |
182 |
AND is_xnack_on_check |
183 |
AND (is_miotensile_check AND is_mlir_check) |
184 |
-diff --color -upr MIOpen-rocm-5.1.3/test/handle_test.cpp gfx1031/test/handle_test.cpp |
185 |
--- MIOpen-rocm-5.1.3/test/handle_test.cpp 2022-05-08 14:08:05.000000000 +0800 |
186 |
+++ gfx1031/test/handle_test.cpp 2022-09-01 18:36:19.018979413 +0800 |
187 |
@@ -234,7 +234,7 @@ void test_warnings(kernel_type_t kern_ty |
188 |
@@ -383,7 +362,6 @@ diff --color -upr MIOpen-rocm-5.1.3/test/handle_test.cpp gfx1031/test/handle_tes |
189 |
auto this_arch = h.GetDeviceName(); |
190 |
EXPECT(std::any_of( |
191 |
known_arch.begin(), known_arch.end(), [&](std::string arch) { return arch == this_arch; })); |
192 |
-diff --color -upr MIOpen-rocm-5.1.3/test/mdgraph.cpp gfx1031/test/mdgraph.cpp |
193 |
--- MIOpen-rocm-5.1.3/test/mdgraph.cpp 2022-05-08 14:08:05.000000000 +0800 |
194 |
+++ gfx1031/test/mdgraph.cpp 2022-09-01 18:36:19.022979405 +0800 |
195 |
@@ -222,7 +222,7 @@ struct mdgraph_driver : test_driver |