Skip to content

Commit 99a228b

Browse files
authored
[SYCL] Revert "Optimize handler::setNDRangeDescriptor" (#18077)
Reverts [#17969](#17969), based on the discussion.
1 parent 5ca1fbe commit 99a228b

File tree

4 files changed

+8
-47
lines changed

4 files changed

+8
-47
lines changed

sycl/include/sycl/detail/array.hpp

Lines changed: 0 additions & 4 deletions
Original file line numberDiff line numberDiff line change
@@ -58,10 +58,6 @@ template <int dimensions = 1> class array {
5858
return result;
5959
}
6060

61-
void reset(size_t value) {
62-
std::fill(common_array, common_array + dimensions, value);
63-
}
64-
6561
size_t get(int dimension) const {
6662
check_dimension(dimension);
6763
return common_array[dimension];

sycl/include/sycl/handler.hpp

Lines changed: 2 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -3687,8 +3687,7 @@ class __SYCL_EXPORT handler {
36873687
bool HasAssociatedAccessor(detail::AccessorImplHost *Req,
36883688
access::target AccessTarget) const;
36893689

3690-
template <int Dims>
3691-
static sycl::range<3> padRange(const sycl::range<Dims> &Range) {
3690+
template <int Dims> static sycl::range<3> padRange(sycl::range<Dims> Range) {
36923691
if constexpr (Dims == 3) {
36933692
return Range;
36943693
} else {
@@ -3699,7 +3698,7 @@ class __SYCL_EXPORT handler {
36993698
}
37003699
}
37013700

3702-
template <int Dims> static sycl::id<3> padId(const sycl::id<Dims> &Id) {
3701+
template <int Dims> static sycl::id<3> padId(sycl::id<Dims> Id) {
37033702
if constexpr (Dims == 3) {
37043703
return Id;
37053704
} else {

sycl/source/detail/cg.hpp

Lines changed: 3 additions & 37 deletions
Original file line numberDiff line numberDiff line change
@@ -115,6 +115,9 @@ class NDRDescT {
115115
setNDRangeLeftover();
116116
}
117117

118+
NDRDescT(sycl::range<3> NumWorkItems, sycl::id<3> Offset, int DimsArg)
119+
: GlobalSize{NumWorkItems}, GlobalOffset{Offset}, Dims{size_t(DimsArg)} {}
120+
118121
template <int Dims_>
119122
NDRDescT(sycl::nd_range<Dims_> ExecutionRange, int DimsArg)
120123
: NDRDescT(padRange(ExecutionRange.get_global_range()),
@@ -141,43 +144,6 @@ class NDRDescT {
141144
ClusterDimensions[I] = (I < Dims) ? N[I] : 1;
142145
}
143146

144-
void reset(const sycl::range<3> &N, bool SetNumWorkGroups, int DimsArg) {
145-
if (SetNumWorkGroups) {
146-
GlobalSize.reset(0);
147-
NumWorkGroups = N;
148-
} else {
149-
GlobalSize = N;
150-
NumWorkGroups.reset(0);
151-
}
152-
LocalSize.reset(0);
153-
GlobalOffset.reset(0);
154-
ClusterDimensions.reset(1);
155-
Dims = size_t(DimsArg);
156-
setNDRangeLeftover();
157-
}
158-
159-
void reset(const sycl::range<3> &NumWorkItems, const sycl::id<3> &Offset,
160-
int DimsArg) {
161-
GlobalSize = NumWorkItems;
162-
GlobalOffset = Offset;
163-
NumWorkGroups.reset(0);
164-
LocalSize.reset(0);
165-
ClusterDimensions.reset(1);
166-
Dims = size_t(DimsArg);
167-
}
168-
169-
void reset(const sycl::range<3> &NumWorkItems,
170-
const sycl::range<3> &LocalSizeArg, const sycl::id<3> &Offset,
171-
int DimsArg) {
172-
GlobalSize = NumWorkItems;
173-
LocalSize = LocalSizeArg;
174-
GlobalOffset = Offset;
175-
NumWorkGroups.reset(0);
176-
ClusterDimensions.reset(1);
177-
Dims = size_t(DimsArg);
178-
setNDRangeLeftover();
179-
}
180-
181147
NDRDescT &operator=(const NDRDescT &Desc) = default;
182148
NDRDescT &operator=(NDRDescT &&Desc) = default;
183149

sycl/source/handler.cpp

Lines changed: 3 additions & 3 deletions
Original file line numberDiff line numberDiff line change
@@ -2218,16 +2218,16 @@ sycl::detail::CGType handler::getType() const { return impl->MCGType; }
22182218

22192219
void handler::setNDRangeDescriptorPadded(sycl::range<3> N,
22202220
bool SetNumWorkGroups, int Dims) {
2221-
impl->MNDRDesc.reset(N, SetNumWorkGroups, Dims);
2221+
impl->MNDRDesc = NDRDescT{N, SetNumWorkGroups, Dims};
22222222
}
22232223
void handler::setNDRangeDescriptorPadded(sycl::range<3> NumWorkItems,
22242224
sycl::id<3> Offset, int Dims) {
2225-
impl->MNDRDesc.reset(NumWorkItems, Offset, Dims);
2225+
impl->MNDRDesc = NDRDescT{NumWorkItems, Offset, Dims};
22262226
}
22272227
void handler::setNDRangeDescriptorPadded(sycl::range<3> NumWorkItems,
22282228
sycl::range<3> LocalSize,
22292229
sycl::id<3> Offset, int Dims) {
2230-
impl->MNDRDesc.reset(NumWorkItems, LocalSize, Offset, Dims);
2230+
impl->MNDRDesc = NDRDescT{NumWorkItems, LocalSize, Offset, Dims};
22312231
}
22322232

22332233
void handler::saveCodeLoc(detail::code_location CodeLoc, bool IsTopCodeLoc) {

0 commit comments

Comments
 (0)