just remove literal from banlist instead

Author: brandon-b-miller

numba_cuda/numba/cuda/__init__.py

@@ -66,33 +66,3 @@
     )
 
 from numba.cuda.np.ufunc import vectorize, guvectorize
-
-
-_lazy_exports = {
-    "literal_unroll": ("numba.cuda.misc.special", "literal_unroll"),
-    "literal": ("numba.cuda.misc", "literal"),
-}
-
-__all__ = list(globals().get("__all__", [])) + list(_lazy_exports.keys())
-
-
-def __getattr__(name):
-    """
-    Lazily import a few attrs that might import lowering
-    """
-    if name in _lazy_exports:
-        mod_name, attr_name = _lazy_exports[name]
-        try:
-            module = importlib.import_module(mod_name)
-            value = getattr(module, attr_name)
-        except Exception as exc:
-            raise ImportError(
-                f"could not import name {attr_name!r} from {mod_name!r}"
-            ) from exc
-        globals()[name] = value
-        return value
-    raise AttributeError(f"module {__name__!r} has no attribute {name!r}")
-
-
-def __dir__():
-    return sorted(set(list(globals().keys()) + list(_lazy_exports.keys())))

numba_cuda/numba/cuda/device_init.py

@@ -87,6 +87,9 @@
     PTXSource,
 )
 
+from numba.cuda.misc.special import literal_unroll
+from numba.cuda.misc import literal
+
 reduce = Reduce = reduction.Reduce
 
 # Expose vector type constructors and aliases as module level attributes.

numba_cuda/numba/cuda/tests/nocuda/test_import.py

@@ -38,7 +38,6 @@ def test_no_impl_import(self):
             "numba.cuda.python.printimpl",
             "numba.cuda.core.optional",
             "numba.cuda.misc.gdb_hook",
-            "numba.cuda.misc.literal",
             "numba.cuda.misc.cffiimpl",
             "numba.np.linalg",
             "numba.np.polynomial",