Skip to content

Commit

Permalink
MAINT: remove DAAL CL kernels and GPU interfaces (#2816)
Browse files Browse the repository at this point in the history
* MAINT: remove daal CL kernels

* removal of non oneapi/ files referencing oneapi/

* remove daal/*/oneapi includes

* remove oneapi::internal references

* alternative include for onedal knn

* removal of logic outside of device.isCpu

* small knn fixes

* restore include sycl table header

* opencl cleanup

* remove cl kernels

* sycl table removal

* remove deviceInfo checks

* remova cpp/daal/src/sycl/*

* knn fixed

* removal of all execution context guard

* delete sycl table adapter

* oops

* swap include

* DAAL_SYCL_INTERFACE removal initial

* clang

* remove daal gpu support checker

* swap include

* re-add bazel build knn daal deps

* clang

* remove exec ctx, services/internal/sycl, clean BUILDs

* broader include swap

* forgot threadcomm

* remove bazel circular depenendency

* clang

* restore thread comm

* removal all daal SYCL container/dispatching macros

* remove python double exit code check

* dpc bazel test fixes

* restore makefile

* more opencl restoration

* samples restore

* restore .ci/env/apt.sh based on discussion

* swap ucapi knn header include

* restore docs with opencl

* remove interop/common_dpc.hpp from new file

* address undefined uint error
  • Loading branch information
ethanglaser committed Aug 12, 2024
1 parent 32b55bd commit e983f90
Show file tree
Hide file tree
Showing 386 changed files with 359 additions and 52,791 deletions.
2 changes: 0 additions & 2 deletions .ci/pipeline/ci.yml
Original file line number Diff line number Diff line change
Expand Up @@ -623,8 +623,6 @@ jobs:
ret_code=0
python -m sklearnex sklearnex/tests/run_examples.py
ret_code=$(($ret_code + $?))
python -m sklearnex sklearnex/tests/daal4py/sycl/sklearn_sycl.py
ret_code=$(($ret_code + $?))
exit $ret_code
displayName: sklearnex examples
- script: |
Expand Down
24 changes: 7 additions & 17 deletions cpp/daal/BUILD
Original file line number Diff line number Diff line change
Expand Up @@ -122,23 +122,6 @@ daal_module(
],
)

daal_module(
name = "sycl",
hdrs = glob(["src/sycl/**/*.h", "src/sycl/**/*.cl"]),
srcs = glob(["src/sycl/**/*.cpp"]),
deps = select({
"@config//:backend_ref": [
":services",
"@onedal//cpp/daal/src/algorithms/engines:kernel",
],
"//conditions:default": [
":services",
"@onedal//cpp/daal/src/algorithms/engines:kernel",
"@micromkl_dpc//:headers",
],
}),
)

daal_module(
name = "threading_tbb",
srcs = glob(["src/threading/**/*.cpp"]),
Expand All @@ -164,6 +147,13 @@ daal_module(
}),
)

daal_module(
name = "engines",
deps = [
"@onedal//cpp/daal/src/algorithms/engines:kernel",
],
)

daal_module(
name = "core",
deps = [
Expand Down
5 changes: 0 additions & 5 deletions cpp/daal/include/algorithms/algorithm_container_base_batch.h
Original file line number Diff line number Diff line change
Expand Up @@ -27,8 +27,6 @@

#include "services/daal_memory.h"
#include "services/internal/daal_kernel_defines.h"
#include "services/internal/gpu_support_checker.h"
#include "services/internal/execution_context.h"

namespace daal
{
Expand Down Expand Up @@ -174,9 +172,6 @@ class DAAL_EXPORT AlgorithmDispatchContainer<batch, RV64Container DAAL_KERNEL_RV

virtual services::Status compute() DAAL_C11_OVERRIDE
{
services::internal::sycl::ExecutionContextIface & context = services::internal::getDefaultContext();
services::internal::sycl::InfoDevice & deviceInfo = context.getInfoDevice();
if (!daal::services::internal::isImplementedForDevice(deviceInfo, _cntr)) return services::Status(services::ErrorDeviceSupportNotImplemented);
_cntr->setArguments(this->_in, this->_res, this->_par, this->_hpar);
return _cntr->compute();
}
Expand Down
5 changes: 0 additions & 5 deletions cpp/daal/include/algorithms/algorithm_container_base_common.h
Original file line number Diff line number Diff line change
Expand Up @@ -29,8 +29,6 @@

#include "algorithms/algorithm_container_base.h"
#include "services/error_handling.h"
#include "services/internal/gpu_support_checker.h"
#include "services/internal/execution_context.h"

namespace daal
{
Expand Down Expand Up @@ -78,9 +76,6 @@ class DAAL_EXPORT AlgorithmDispatchContainer : public AlgorithmContainerImpl<mod

virtual services::Status compute() DAAL_C11_OVERRIDE
{
services::internal::sycl::ExecutionContextIface & context = services::internal::getDefaultContext();
services::internal::sycl::InfoDevice & deviceInfo = context.getInfoDevice();
if (!daal::services::internal::isImplementedForDevice(deviceInfo, _cntr)) return services::Status(services::ErrorDeviceSupportNotImplemented);
_cntr->setArguments(this->_in, this->_pres, this->_par, this->_hpar);
return _cntr->compute();
}
Expand Down
57 changes: 0 additions & 57 deletions cpp/daal/include/daal_sycl.h

This file was deleted.

This file was deleted.

Loading

0 comments on commit e983f90

Please sign in to comment.