diff --git a/numba_cuda/numba/cuda/testing.py b/numba_cuda/numba/cuda/testing.py index 745514a9f..7e3cd6f85 100644 --- a/numba_cuda/numba/cuda/testing.py +++ b/numba_cuda/numba/cuda/testing.py @@ -35,14 +35,6 @@ def tearDown(self): config.CUDA_LOW_OCCUPANCY_WARNINGS = self._low_occupancy_warnings config.CUDA_WARN_ON_IMPLICIT_COPY = self._warn_on_implicit_copy - def skip_if_lto(self, reason): - # Some linkers need the compute capability to be specified, so we - # always specify it here. - cc = devices.get_context().device.compute_capability - linker = driver._Linker.new(cc=cc) - if linker.lto: - self.skipTest(reason) - class ContextResettingTestCase(CUDATestCase): """ diff --git a/numba_cuda/numba/cuda/tests/cudapy/test_debuginfo.py b/numba_cuda/numba/cuda/tests/cudapy/test_debuginfo.py index 9bccf9856..93c6a5987 100644 --- a/numba_cuda/numba/cuda/tests/cudapy/test_debuginfo.py +++ b/numba_cuda/numba/cuda/tests/cudapy/test_debuginfo.py @@ -14,15 +14,6 @@ class TestCudaDebugInfo(CUDATestCase): These tests only checks the compiled PTX for debuginfo section """ - def setUp(self): - super().setUp() - # If we're using LTO then we can't check the PTX in these tests, - # because we produce LTO-IR, which is opaque to the user. - # Additionally, LTO optimizes away the exception status due to an - # oversight in the way we generate it (it is not added to the used - # list). - self.skip_if_lto("Exceptions not supported with LTO") - def _getasm(self, fn, sig): fn.compile(sig) return fn.inspect_asm(sig) diff --git a/numba_cuda/numba/cuda/tests/cudapy/test_exception.py b/numba_cuda/numba/cuda/tests/cudapy/test_exception.py index 63dce76eb..87f16608e 100644 --- a/numba_cuda/numba/cuda/tests/cudapy/test_exception.py +++ b/numba_cuda/numba/cuda/tests/cudapy/test_exception.py @@ -6,12 +6,6 @@ class TestException(CUDATestCase): - def setUp(self): - super().setUp() - # LTO optimizes away the exception status due to an oversight - # in the way we generate it (it is not added to the used list). - self.skip_if_lto("Exceptions not supported with LTO") - def test_exception(self): def foo(ary): x = cuda.threadIdx.x diff --git a/numba_cuda/numba/cuda/tests/cudapy/test_fastmath.py b/numba_cuda/numba/cuda/tests/cudapy/test_fastmath.py index 543ddd108..f30526376 100644 --- a/numba_cuda/numba/cuda/tests/cudapy/test_fastmath.py +++ b/numba_cuda/numba/cuda/tests/cudapy/test_fastmath.py @@ -188,10 +188,6 @@ def test_divf(self): ) def test_divf_exception(self): - # LTO optimizes away the exception status due to an oversight - # in the way we generate it (it is not added to the used list). - self.skip_if_lto("Exceptions not supported with LTO") - def f10(r, x, y): r[0] = x / y diff --git a/numba_cuda/numba/cuda/tests/cudapy/test_userexc.py b/numba_cuda/numba/cuda/tests/cudapy/test_userexc.py index b444c9155..06c6cc6eb 100644 --- a/numba_cuda/numba/cuda/tests/cudapy/test_userexc.py +++ b/numba_cuda/numba/cuda/tests/cudapy/test_userexc.py @@ -13,13 +13,6 @@ class MyError(Exception): class TestUserExc(CUDATestCase): - def setUp(self): - super().setUp() - # LTO optimizes away the exception status due to an oversight - # in the way we generate it (it is not added to the used list). - # See https://github.com/numba/numba/issues/9526. - self.skip_if_lto("Exceptions not supported with LTO") - def test_user_exception(self): @cuda.jit("void(int32)", debug=True, opt=False) def test_exc(x):