Skip to content

Commit 4c042dd

Browse files
AntonyvanceAntonyvance
authored
Merge branch 'main' into rajprinc/unit-test-new-api-changes
2 parents 548b840 + 0b4b770 commit 4c042dd

File tree

66 files changed

+3510
-543
lines changed

Some content is hidden

Large Commits have some content hidden by default. Use the searchbox below for content that may be hidden.

66 files changed

+3510
-543
lines changed

‎.github/workflows/xe_benchmarks_ondemand.yml‎

Lines changed: 3 additions & 0 deletions
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,9 @@
11
name: "SYCL-TLA Benchmarks"
22

33
on:
4+
schedule:
5+
# Runs at 00:00 AM UTC on Wednesday and Friday
6+
- cron: '0 0 * * 3,5'
47
workflow_dispatch:
58

69
permissions: {}

‎examples/00_bmg_gemm/00_bmg_gemm.cpp‎

Lines changed: 17 additions & 9 deletions
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,6 @@
11
/***************************************************************************************************
2-
* Copyright (c) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3-
* Copyright (C) 2025 Intel Corporation, All rights reserved.
2+
* Copyright (C) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3+
* Copyright (C) 2025 -2026 Intel Corporation, All rights reserved.
44
* SPDX-License-Identifier: BSD-3-Clause
55
*
66
* Redistribution and use in source and binary forms, with or without
@@ -89,13 +89,13 @@ struct Options {
8989
bool help;
9090
bool error;
9191

92-
int m, n, k, l, iterations;
92+
int m, n, k, l, iterations, verify;
9393
float alpha, beta;
9494

9595
Options():
9696
help(false),
9797
error(false),
98-
m(5120), n(4096), k(4096), l(1), iterations(20),
98+
m(5120), n(4096), k(4096), l(1), iterations(20), verify(1),
9999
alpha(1.f), beta(0.f)
100100
{ }
101101

@@ -115,6 +115,7 @@ struct Options {
115115
cmd.get_cmd_line_argument("alpha", alpha, 1.f);
116116
cmd.get_cmd_line_argument("beta", beta, 0.f);
117117
cmd.get_cmd_line_argument("iterations", iterations, 100);
118+
cmd.get_cmd_line_argument("verify", verify, 1);
118119
}
119120

120121
/// Prints the usage statement.
@@ -129,7 +130,8 @@ struct Options {
129130
<< " --l=<int> Sets the L extent (batch count) of the GEMM\n"
130131
<< " --alpha=<s32> Epilogue scalar alpha\n"
131132
<< " --beta=<s32> Epilogue scalar beta\n\n"
132-
<< " --iterations=<int> Iterations\n\n";
133+
<< " --iterations=<int> Iterations\n\n"
134+
<< " --verify=<int> Specify whether to verify.\n\n";
133135

134136
return out;
135137
}
@@ -272,11 +274,17 @@ struct ExampleRunner {
272274

273275
compat::wait();
274276

275-
// Verify that the result is correct
276-
bool passed = verify(problem_size, options.alpha, options.beta);
277-
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
277+
if (options.verify != 0) {
278+
// Verify that the result is correct
279+
bool passed = verify(problem_size, options.alpha, options.beta);
280+
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
278281

279-
if (passed && options.iterations > 0) {
282+
if (!passed) return cutlass::Status::kErrorInternal;
283+
} else {
284+
std::cout << "Disposition is skipped." << std::endl;
285+
}
286+
287+
if (options.iterations > 0) {
280288
GPU_Clock timer;
281289
timer.start();
282290
for (int i = 0; i < options.iterations; ++i) {

‎examples/00_bmg_gemm/00_bmg_gemm_padded.cpp‎

Lines changed: 15 additions & 9 deletions
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,6 @@
11
/***************************************************************************************************
2-
* Copyright (c) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3-
* Copyright (C) 2025 Intel Corporation, All rights reserved.
2+
* Copyright (C) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3+
* Copyright (C) 2025 - 2026 Intel Corporation, All rights reserved.
44
* SPDX-License-Identifier: BSD-3-Clause
55
*
66
* Redistribution and use in source and binary forms, with or without
@@ -96,13 +96,13 @@ struct Options {
9696
bool help;
9797
bool error;
9898

99-
int m, n, k, l, iterations;
99+
int m, n, k, l, iterations, verify;
100100
float alpha, beta;
101101

102102
Options():
103103
help(false),
104104
error(false),
105-
m(5120), n(4096), k(4096), l(1), iterations(20),
105+
m(5120), n(4096), k(4096), l(1), iterations(20), verify(1),
106106
alpha(1.f), beta(0.f)
107107
{ }
108108

@@ -122,6 +122,7 @@ struct Options {
122122
cmd.get_cmd_line_argument("alpha", alpha, 1.f);
123123
cmd.get_cmd_line_argument("beta", beta, 0.f);
124124
cmd.get_cmd_line_argument("iterations", iterations, 100);
125+
cmd.get_cmd_line_argument("verify", verify, 1);
125126
}
126127

127128
/// Prints the usage statement.
@@ -136,7 +137,8 @@ struct Options {
136137
<< " --l=<int> Sets the L extent (batch count) of the GEMM\n"
137138
<< " --alpha=<s32> Epilogue scalar alpha\n"
138139
<< " --beta=<s32> Epilogue scalar beta\n\n"
139-
<< " --iterations=<int> Iterations\n\n";
140+
<< " --iterations=<int> Iterations\n\n"
141+
<< " --verify=<int> Specify whether to verify.\n\n";
140142

141143
return out;
142144
}
@@ -311,11 +313,15 @@ struct ExampleRunner {
311313

312314
compat::wait();
313315

314-
// Verify that the result is correct
315-
bool passed = verify(problem_size, options.alpha, options.beta);
316-
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
316+
if (options.verify != 0) {
317+
// Verify that the result is correct
318+
bool passed = verify(problem_size, options.alpha, options.beta);
319+
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
317320

318-
if(!passed) return cutlass::Status::kErrorInternal;
321+
if (!passed) return cutlass::Status::kErrorInternal;
322+
} else {
323+
std::cout << "Disposition is skipped." << std::endl;
324+
}
319325

320326
if (options.iterations > 0) {
321327
GPU_Clock timer;

‎examples/00_bmg_gemm/00_bmg_gemm_with_sycl_queue.cpp‎

Lines changed: 15 additions & 9 deletions
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,6 @@
11
/***************************************************************************************************
2-
* Copyright (c) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3-
* Copyright (C) 2025 Intel Corporation, All rights reserved.
2+
* Copyright (C) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3+
* Copyright (C) 2025 - 2026 Intel Corporation, All rights reserved.
44
* SPDX-License-Identifier: BSD-3-Clause
55
*
66
* Redistribution and use in source and binary forms, with or without
@@ -71,13 +71,13 @@ struct Options {
7171
bool help;
7272
bool error;
7373

74-
int m, n, k, l, iterations;
74+
int m, n, k, l, iterations, verify;
7575
float alpha, beta;
7676

7777
Options():
7878
help(false),
7979
error(false),
80-
m(5120), n(4096), k(4096), l(1), iterations(20),
80+
m(5120), n(4096), k(4096), l(1), iterations(20), verify(1),
8181
alpha(1.f), beta(0.f)
8282
{ }
8383

@@ -97,6 +97,7 @@ struct Options {
9797
cmd.get_cmd_line_argument("alpha", alpha, 1.f);
9898
cmd.get_cmd_line_argument("beta", beta, 0.f);
9999
cmd.get_cmd_line_argument("iterations", iterations, 100);
100+
cmd.get_cmd_line_argument("verify", verify, 1);
100101
}
101102

102103
/// Prints the usage statement.
@@ -111,7 +112,8 @@ struct Options {
111112
<< " --l=<int> Sets the L extent (batch count) of the GEMM\n"
112113
<< " --alpha=<s32> Epilogue scalar alpha\n"
113114
<< " --beta=<s32> Epilogue scalar beta\n\n"
114-
<< " --iterations=<int> Iterations\n\n";
115+
<< " --iterations=<int> Iterations\n\n"
116+
<< " --verify=<int> Specify whether to verify.\n\n";
115117

116118
return out;
117119
}
@@ -274,11 +276,15 @@ struct ExampleRunner {
274276

275277
q.wait_and_throw();
276278

277-
// Verify that the result is correct
278-
bool passed = verify(mem, problem_size, options.alpha, options.beta);
279-
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
279+
if (options.verify != 0) {
280+
// Verify that the result is correct
281+
bool passed = verify(mem, problem_size, options.alpha, options.beta);
282+
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
280283

281-
if(!passed) return cutlass::Status::kErrorInternal;
284+
if (!passed) return cutlass::Status::kErrorInternal;
285+
} else {
286+
std::cout << "Disposition is skipped." << std::endl;
287+
}
282288

283289
if (options.iterations > 0) {
284290
GPU_Clock timer;

‎examples/00_bmg_gemm/legacy/00_bmg_gemm.cpp‎

Lines changed: 15 additions & 9 deletions
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,6 @@
11
/***************************************************************************************************
2-
* Copyright (c) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3-
* Copyright (C) 2025 Intel Corporation, All rights reserved.
2+
* Copyright (C) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3+
* Copyright (C) 2025 - 2026 Intel Corporation, All rights reserved.
44
* SPDX-License-Identifier: BSD-3-Clause
55
*
66
* Redistribution and use in source and binary forms, with or without
@@ -89,14 +89,14 @@ struct Options {
8989
bool help;
9090
bool error;
9191

92-
int m, n, k, l, iterations;
92+
int m, n, k, l, iterations, verify;
9393
float alpha, beta;
9494

9595
Options():
9696
help(false),
9797
error(false),
9898
m(5120), n(4096), k(4096), l(1), iterations(20),
99-
alpha(1.f), beta(0.f)
99+
alpha(1.f), beta(0.f), verify(1)
100100
{ }
101101

102102
// Parses the command line
@@ -115,6 +115,7 @@ struct Options {
115115
cmd.get_cmd_line_argument("alpha", alpha, 1.f);
116116
cmd.get_cmd_line_argument("beta", beta, 0.f);
117117
cmd.get_cmd_line_argument("iterations", iterations, 100);
118+
cmd.get_cmd_line_argument("verify", verify, 1);
118119
}
119120

120121
/// Prints the usage statement.
@@ -129,7 +130,8 @@ struct Options {
129130
<< " --l=<int> Sets the L extent (batch count) of the GEMM\n"
130131
<< " --alpha=<s32> Epilogue scalar alpha\n"
131132
<< " --beta=<s32> Epilogue scalar beta\n\n"
132-
<< " --iterations=<int> Iterations\n\n";
133+
<< " --iterations=<int> Iterations\n\n"
134+
<< " --verify=<int> Specify whether to verify.\n\n";
133135

134136
return out;
135137
}
@@ -273,11 +275,15 @@ struct ExampleRunner {
273275

274276
compat::wait();
275277

276-
// Verify that the result is correct
277-
bool passed = verify(problem_size, options.alpha, options.beta);
278-
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
278+
if (options.verify != 0) {
279+
// Verify that the result is correct
280+
bool passed = verify(problem_size, options.alpha, options.beta);
281+
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
279282

280-
if(!passed) return cutlass::Status::kErrorInternal;
283+
if(!passed) return cutlass::Status::kErrorInternal;
284+
} else {
285+
std::cout << "Disposition is skipped." << std::endl;
286+
}
281287

282288
if (options.iterations > 0) {
283289
GPU_Clock timer;

‎examples/00_bmg_gemm/legacy/00_bmg_gemm_padded.cpp‎

Lines changed: 15 additions & 9 deletions
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,6 @@
11
/***************************************************************************************************
2-
* Copyright (c) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3-
* Copyright (C) 2025 Intel Corporation, All rights reserved.
2+
* Copyright (C) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3+
* Copyright (C) 2025 - 2026 Intel Corporation, All rights reserved.
44
* SPDX-License-Identifier: BSD-3-Clause
55
*
66
* Redistribution and use in source and binary forms, with or without
@@ -96,14 +96,14 @@ struct Options {
9696
bool help;
9797
bool error;
9898

99-
int m, n, k, l, iterations;
99+
int m, n, k, l, iterations, verify;
100100
float alpha, beta;
101101

102102
Options():
103103
help(false),
104104
error(false),
105105
m(5120), n(4096), k(4096), l(1), iterations(20),
106-
alpha(1.f), beta(0.f)
106+
alpha(1.f), beta(0.f), verify(1)
107107
{ }
108108

109109
// Parses the command line
@@ -122,6 +122,7 @@ struct Options {
122122
cmd.get_cmd_line_argument("alpha", alpha, 1.f);
123123
cmd.get_cmd_line_argument("beta", beta, 0.f);
124124
cmd.get_cmd_line_argument("iterations", iterations, 100);
125+
cmd.get_cmd_line_argument("verify", verify, 1);
125126
}
126127

127128
/// Prints the usage statement.
@@ -136,7 +137,8 @@ struct Options {
136137
<< " --l=<int> Sets the L extent (batch count) of the GEMM\n"
137138
<< " --alpha=<s32> Epilogue scalar alpha\n"
138139
<< " --beta=<s32> Epilogue scalar beta\n\n"
139-
<< " --iterations=<int> Iterations\n\n";
140+
<< " --iterations=<int> Iterations\n\n"
141+
<< " --verify=<int> Specify whether to verify.\n\n";
140142

141143
return out;
142144
}
@@ -311,11 +313,15 @@ struct ExampleRunner {
311313

312314
compat::wait();
313315

314-
// Verify that the result is correct
315-
bool passed = verify(problem_size, options.alpha, options.beta);
316-
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
316+
if (options.verify != 0) {
317+
// Verify that the result is correct
318+
bool passed = verify(problem_size, options.alpha, options.beta);
319+
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
317320

318-
if(!passed) return cutlass::Status::kErrorInternal;
321+
if(!passed) return cutlass::Status::kErrorInternal;
322+
} else {
323+
std::cout << "Disposition is skipped." << std::endl;
324+
}
319325

320326
if (options.iterations > 0) {
321327
GPU_Clock timer;

‎examples/00_bmg_gemm/legacy/00_bmg_gemm_with_sycl_queue.cpp‎

Lines changed: 15 additions & 9 deletions
Original file line numberDiff line numberDiff line change
@@ -1,6 +1,6 @@
11
/***************************************************************************************************
2-
* Copyright (c) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3-
* Copyright (C) 2025 Intel Corporation, All rights reserved.
2+
* Copyright (C) 2024 - 2024 Codeplay Software Ltd. All rights reserved.
3+
* Copyright (C) 2025 - 2026 Intel Corporation, All rights reserved.
44
* SPDX-License-Identifier: BSD-3-Clause
55
*
66
* Redistribution and use in source and binary forms, with or without
@@ -71,14 +71,14 @@ struct Options {
7171
bool help;
7272
bool error;
7373

74-
int m, n, k, l, iterations;
74+
int m, n, k, l, iterations, verify;
7575
float alpha, beta;
7676

7777
Options():
7878
help(false),
7979
error(false),
8080
m(5120), n(4096), k(4096), l(1), iterations(20),
81-
alpha(1.f), beta(0.f)
81+
alpha(1.f), beta(0.f), verify(1)
8282
{ }
8383

8484
// Parses the command line
@@ -97,6 +97,7 @@ struct Options {
9797
cmd.get_cmd_line_argument("alpha", alpha, 1.f);
9898
cmd.get_cmd_line_argument("beta", beta, 0.f);
9999
cmd.get_cmd_line_argument("iterations", iterations, 100);
100+
cmd.get_cmd_line_argument("verify", verify, 1);
100101
}
101102

102103
/// Prints the usage statement.
@@ -111,7 +112,8 @@ struct Options {
111112
<< " --l=<int> Sets the L extent (batch count) of the GEMM\n"
112113
<< " --alpha=<s32> Epilogue scalar alpha\n"
113114
<< " --beta=<s32> Epilogue scalar beta\n\n"
114-
<< " --iterations=<int> Iterations\n\n";
115+
<< " --iterations=<int> Iterations\n\n"
116+
<< " --verify=<int> Specify whether to verify.\n\n";
115117

116118
return out;
117119
}
@@ -275,11 +277,15 @@ struct ExampleRunner {
275277

276278
q.wait_and_throw();
277279

278-
// Verify that the result is correct
279-
bool passed = verify(mem, problem_size, options.alpha, options.beta);
280-
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
280+
if (options.verify != 0) {
281+
// Verify that the result is correct
282+
bool passed = verify(mem, problem_size, options.alpha, options.beta);
283+
std::cout << "Disposition: " << (passed ? "Passed" : "Failed") << std::endl;
281284

282-
if(!passed) return cutlass::Status::kErrorInternal;
285+
if(!passed) return cutlass::Status::kErrorInternal;
286+
} else {
287+
std::cout << "Disposition is skipped." << std::endl;
288+
}
283289

284290
if (options.iterations > 0) {
285291
GPU_Clock timer;

0 commit comments

Comments
 (0)