2024-03-19 11:12:25 +08:00
|
|
|
// Copyright © 2023-2024 Apple Inc.
|
2023-11-30 02:42:59 +08:00
|
|
|
|
|
|
|
#include "mlx/backend/metal/metal.h"
|
2024-03-19 11:12:25 +08:00
|
|
|
#include <nanobind/nanobind.h>
|
2023-11-30 02:42:59 +08:00
|
|
|
|
2024-03-19 11:12:25 +08:00
|
|
|
namespace nb = nanobind;
|
|
|
|
using namespace nb::literals;
|
2023-11-30 02:42:59 +08:00
|
|
|
|
|
|
|
using namespace mlx::core;
|
|
|
|
|
2024-03-19 11:12:25 +08:00
|
|
|
void init_metal(nb::module_& m) {
|
|
|
|
nb::module_ metal = m.def_submodule("metal", "mlx.metal");
|
2024-01-19 00:33:34 +08:00
|
|
|
metal.def(
|
2024-03-02 11:51:58 +08:00
|
|
|
"is_available",
|
|
|
|
&metal::is_available,
|
|
|
|
R"pbdoc(
|
|
|
|
Check if the Metal back-end is available.
|
|
|
|
)pbdoc");
|
2024-01-19 00:33:34 +08:00
|
|
|
metal.def(
|
2024-03-02 11:51:58 +08:00
|
|
|
"get_active_memory",
|
|
|
|
&metal::get_active_memory,
|
|
|
|
R"pbdoc(
|
|
|
|
Get the actively used memory in bytes.
|
|
|
|
|
|
|
|
Note, this will not always match memory use reported by the system because
|
|
|
|
it does not include cached memory buffers.
|
|
|
|
)pbdoc");
|
|
|
|
metal.def(
|
|
|
|
"get_peak_memory",
|
|
|
|
&metal::get_peak_memory,
|
|
|
|
R"pbdoc(
|
|
|
|
Get the peak amount of used memory in bytes.
|
|
|
|
|
|
|
|
The maximum memory used is recorded from the beginning of the program
|
|
|
|
execution.
|
|
|
|
)pbdoc");
|
|
|
|
metal.def(
|
|
|
|
"get_cache_memory",
|
|
|
|
&metal::get_cache_memory,
|
|
|
|
R"pbdoc(
|
|
|
|
Get the cache size in bytes.
|
|
|
|
|
|
|
|
The cache includes memory not currently used that has not been returned
|
|
|
|
to the system allocator.
|
|
|
|
)pbdoc");
|
|
|
|
metal.def(
|
|
|
|
"set_memory_limit",
|
|
|
|
&metal::set_memory_limit,
|
|
|
|
"limit"_a,
|
2024-03-19 11:12:25 +08:00
|
|
|
nb::kw_only(),
|
2024-03-02 11:51:58 +08:00
|
|
|
"relaxed"_a = true,
|
|
|
|
R"pbdoc(
|
|
|
|
Set the memory limit.
|
|
|
|
|
|
|
|
Memory allocations will wait on scheduled tasks to complete if the limit
|
|
|
|
is exceeded. If there are no more scheduled tasks an error will be raised
|
|
|
|
if ``relaxed`` is ``False``. Otherwise memory will be allocated
|
|
|
|
(including the potential for swap) if ``relaxed`` is ``True``.
|
|
|
|
|
|
|
|
The memory limit defaults to 1.5 times the maximum recommended working set
|
|
|
|
size reported by the device.
|
|
|
|
|
|
|
|
Args:
|
|
|
|
limit (int): Memory limit in bytes.
|
|
|
|
relaxed (bool, optional): If `False`` an error is raised if the limit
|
|
|
|
is exceeded. Default: ``True``
|
|
|
|
|
|
|
|
Returns:
|
|
|
|
int: The previous memory limit in bytes.
|
|
|
|
)pbdoc");
|
|
|
|
metal.def(
|
|
|
|
"set_cache_limit",
|
|
|
|
&metal::set_cache_limit,
|
|
|
|
"limit"_a,
|
|
|
|
R"pbdoc(
|
|
|
|
Set the free cache limit.
|
|
|
|
|
|
|
|
If using more than the given limit, free memory will be reclaimed
|
|
|
|
from the cache on the next allocation. To disable the cache, set
|
|
|
|
the limit to ``0``.
|
|
|
|
|
|
|
|
The cache limit defaults to the memory limit. See
|
|
|
|
:func:`set_memory_limit` for more details.
|
|
|
|
|
|
|
|
Args:
|
|
|
|
limit (int): The cache limit in bytes.
|
|
|
|
|
|
|
|
Returns:
|
|
|
|
int: The previous cache limit in bytes.
|
|
|
|
)pbdoc");
|
2023-11-30 02:42:59 +08:00
|
|
|
}
|