Block-Structured AMR Software Framework
Loading...
Searching...
No Matches
AMReX_Arena.H
Go to the documentation of this file.
1#ifndef AMREX_ARENA_H_
2#define AMREX_ARENA_H_
3#include <AMReX_Config.H>
4
10#include <AMReX_BLassert.H>
11#include <AMReX_INT.H>
12#ifdef AMREX_USE_GPU
13#include <AMReX_GpuControl.H>
14#endif
15
16#ifdef AMREX_TINY_PROFILING
17#include <AMReX_TinyProfiler.H>
18#else
19namespace amrex {
20 struct MemStat {};
21}
22#endif
23
24#include <cstddef>
25#include <cstdlib>
26#include <limits>
27#include <map>
28#include <mutex>
29#include <unordered_map>
30#include <utility>
31
32namespace amrex {
33
38inline std::size_t aligned_size (std::size_t align_requirement, std::size_t size) noexcept
39{
40 return ((size + (align_requirement-1)) / align_requirement) * align_requirement;
41}
42
45inline bool is_aligned (const void* p, std::size_t alignment) noexcept
46{
47 auto* q = const_cast<void*>(p);
48 auto space = alignment;
49 return std::align(alignment, alignment, q, space) == p;
50}
51
52class Arena;
53
56Arena* The_Arena ();
59Arena* The_Async_Arena ();
63Arena* The_Device_Arena ();
67Arena* The_Managed_Arena ();
70Arena* The_Pinned_Arena ();
74Arena* The_Comms_Arena ();
77Arena* The_Cpu_Arena ();
78
82Arena* The_Null_Arena ();
83
91{
92 Long release_threshold = std::numeric_limits<Long>::max();
93 bool use_cpu_memory = false;
95 bool device_set_readonly = false;
96 bool device_set_preferred = false;
97 bool device_use_hostalloc = false;
98 bool defragmentation = false;
102 return *this;
103 }
107 device_use_hostalloc = false;
108 return *this;
109 }
111 ArenaInfo& SetReadOnly () noexcept {
113 device_set_readonly = true;
114 return *this;
115 }
117 ArenaInfo& SetPreferred () noexcept {
120 return *this;
121 }
123 ArenaInfo& SetHostAlloc () noexcept {
126 return *this;
127 }
129 ArenaInfo& SetCpuMemory () noexcept {
130 use_cpu_memory = true;
132 device_set_readonly = false;
133 device_set_preferred = false;
134 device_use_hostalloc = false;
135 return *this;
136 }
138 ArenaInfo& SetDefragmentation (bool b) noexcept {
139 defragmentation = b;
140 return *this;
141 }
142};
143
152class Arena
153{
154public:
155
156 virtual ~Arena () = default;
157 Arena () noexcept = default;
158
159 Arena (const Arena& rhs) = delete;
160 Arena (Arena&& rhs) = delete;
161 Arena& operator= (const Arena& rhs) = delete;
162 Arena& operator= (Arena&& rhs) = delete;
163
169 [[nodiscard]] virtual void* alloc (std::size_t sz) = 0;
170
185 [[nodiscard]] virtual std::pair<void*,std::size_t>
186 alloc_in_place (void* pt, std::size_t szmin, std::size_t szmax)
187 {
188 ignore_unused(pt, szmin);
189 auto* p = alloc(szmax);
190 return std::make_pair(p, szmax);
191 }
192
205 [[nodiscard]] virtual void*
206 shrink_in_place (void* pt, std::size_t sz)
207 {
208 ignore_unused(pt);
209 return alloc(sz);
210 }
211
213 virtual void free (void* pt) = 0;
214
219 virtual std::size_t freeUnused () { return 0; }
220
226 [[nodiscard]] virtual std::size_t largestFreeBlock () const { return 0; }
227
230 [[nodiscard]] virtual bool isDeviceAccessible () const;
231
234 [[nodiscard]] virtual bool isHostAccessible () const;
235
243 [[nodiscard]] virtual bool isManaged () const;
244
252 [[nodiscard]] virtual bool isDevice () const;
253
261 [[nodiscard]] virtual bool isPinned () const;
262
270 [[nodiscard]] virtual bool hasFreeDeviceMemory (std::size_t sz);
271
276 void registerForProfiling (const std::string& memory_name);
277
283
284#ifdef AMREX_USE_GPU
286 [[nodiscard]] virtual bool isStreamOrderedArena () const { return false; }
287 virtual void streamOrderedFree (void* pt, gpuStream_t stream);
288#endif
289
293 static std::size_t align (std::size_t sz);
294
299 static void Initialize (bool minimal);
300
316 static void PrintUsage (bool print_max_usage=false);
317
329 static void PrintUsageToStream (std::ostream& os, std::string const& space);
330
343 static void PrintUsageToFiles (std::string const& filename, std::string const& message);
344
345 static void Finalize ();
346
355 static const std::size_t align_size = 256;
356
360 [[nodiscard]] const ArenaInfo& arenaInfo () const { return arena_info; }
361
364 virtual void ResetMaxUsageCounter () {}
365
367 [[nodiscard]] static bool IsInitialized ();
368
369protected:
370
372
373 virtual std::size_t freeUnused_protected () { return 0; }
374 void* allocate_system (std::size_t nbytes);
375 void deallocate_system (void* p, std::size_t nbytes);
376 static void out_of_memory_abort (std::string const& memory_type, std::size_t nbytes,
377 std::string const& error_msg);
378
380 struct ArenaProfiler {
382 bool m_do_profiling = false;
384 std::mutex m_arena_profiler_mutex;
386 std::map<std::string, MemStat> m_profiling_stats;
388 std::unordered_map<void*, std::pair<MemStat*, std::size_t>> m_currently_allocated;
389
390 ~ArenaProfiler ();
391 ArenaProfiler () noexcept = default;
392 ArenaProfiler (const ArenaProfiler& rhs) = delete;
393 ArenaProfiler (ArenaProfiler&& rhs) = delete;
394 ArenaProfiler& operator= (const ArenaProfiler& rhs) = delete;
395 ArenaProfiler& operator= (ArenaProfiler&& rhs) = delete;
396
397 void profile_alloc (void* ptr, std::size_t nbytes);
398
399 void profile_free (void* ptr);
400
401 } m_profiler;
403};
404
405}
406
407#endif /*BL_ARENA_H*/
Assertion macros used across AMReX for runtime consistency checks.
#define BL_ASSERT(EX)
Definition AMReX_BLassert.H:39
Abstract base class for memory arenas.
Definition AMReX_Arena.H:153
virtual std::size_t largestFreeBlock() const
Return the largest free memory block already held by this Arena.
Definition AMReX_Arena.H:226
static void Finalize()
Used internally by amrex.
Definition AMReX_Arena.cpp:754
virtual void free(void *pt)=0
Free a previously allocated block pointed to by pt.
virtual void * alloc(std::size_t sz)=0
Allocate sz bytes from this arena.
virtual std::pair< void *, std::size_t > alloc_in_place(void *pt, std::size_t szmin, std::size_t szmax)
Allocate memory in-place if possible.
Definition AMReX_Arena.H:186
static std::size_t align(std::size_t sz)
Return the smallest multiple of Arena::align_size that is >= sz bytes.
Definition AMReX_Arena.cpp:167
Arena() noexcept=default
virtual ~Arena()=default
virtual bool isPinned() const
Check whether it is pinned host memory.
Definition AMReX_Arena.cpp:112
virtual void ResetMaxUsageCounter()
Definition AMReX_Arena.H:364
virtual bool isHostAccessible() const
Definition AMReX_Arena.cpp:76
virtual bool isStreamOrderedArena() const
Is this GPU stream ordered memory allocator?
Definition AMReX_Arena.H:286
static const std::size_t align_size
Definition AMReX_Arena.H:355
static bool IsInitialized()
Definition AMReX_Arena.cpp:814
const ArenaInfo & arenaInfo() const
Return the ArenaInfo object for querying.
Definition AMReX_Arena.H:360
virtual bool isManaged() const
Check whether it is managed GPU memory.
Definition AMReX_Arena.cpp:88
void deregisterFromProfiling()
Remove this Arena from the list of Arenas that are profiled by TinyProfiler. This is equivalent to de...
Definition AMReX_Arena.cpp:154
static void out_of_memory_abort(std::string const &memory_type, std::size_t nbytes, std::string const &error_msg)
Definition AMReX_Arena.cpp:726
virtual std::size_t freeUnused_protected()
Definition AMReX_Arena.H:373
virtual void * shrink_in_place(void *pt, std::size_t sz)
Shrink allocation size in-place.
Definition AMReX_Arena.H:206
virtual void streamOrderedFree(void *pt, gpuStream_t stream)
Definition AMReX_Arena.cpp:130
void registerForProfiling(const std::string &memory_name)
Add this Arena to the list of Arenas that are profiled by TinyProfiler.
Definition AMReX_Arena.cpp:144
static void PrintUsageToFiles(std::string const &filename, std::string const &message)
Print memory usage information of all arenas to given file.
Definition AMReX_Arena.cpp:710
virtual bool isDevice() const
Check whether it is non-managed GPU device memory.
Definition AMReX_Arena.cpp:100
virtual bool hasFreeDeviceMemory(std::size_t sz)
Does the device have enough free memory for allocating this much memory? For CPU builds,...
Definition AMReX_Arena.cpp:123
void deallocate_system(void *p, std::size_t nbytes)
Definition AMReX_Arena.cpp:360
static void Initialize(bool minimal)
Initialize the Arena subsystem (used internally by AMReX).
Definition AMReX_Arena.cpp:409
static void PrintUsage(bool print_max_usage=false)
Print memory usage information of all arenas.
Definition AMReX_Arena.cpp:603
virtual std::size_t freeUnused()
Release unused cached memory back to the system.
Definition AMReX_Arena.H:219
ArenaInfo arena_info
Definition AMReX_Arena.H:371
static void PrintUsageToStream(std::ostream &os, std::string const &space)
Print memory usage information of all arenas to a given output stream.
Definition AMReX_Arena.cpp:666
virtual bool isDeviceAccessible() const
Definition AMReX_Arena.cpp:66
void * allocate_system(std::size_t nbytes)
Definition AMReX_Arena.cpp:173
amrex_long Long
Definition AMReX_INT.H:30
bool is_aligned(const void *p, std::size_t alignment) noexcept
Definition AMReX_Arena.H:45
Arena * The_Managed_Arena()
Definition AMReX_Arena.cpp:850
Arena * The_Comms_Arena()
Definition AMReX_Arena.cpp:880
Arena * The_Device_Arena()
Definition AMReX_Arena.cpp:840
Arena * The_Pinned_Arena()
Definition AMReX_Arena.cpp:860
Arena * The_Async_Arena()
Definition AMReX_Arena.cpp:830
std::size_t aligned_size(std::size_t align_requirement, std::size_t size) noexcept
Return the smallest multiple of align_requirement that is >= size.
Definition AMReX_Arena.H:38
Arena * The_Cpu_Arena()
Definition AMReX_Arena.cpp:870
Arena * The_Arena()
Definition AMReX_Arena.cpp:820
Definition AMReX_Amr.cpp:50
__host__ __device__ void ignore_unused(const Ts &...)
No-op helper that marks variables as intentionally unused.
Definition AMReX.H:259
Arena * The_Null_Arena()
Definition AMReX_Arena.cpp:890
cudaStream_t gpuStream_t
Definition AMReX_GpuControl.H:79
Configuration options for constructing an Arena.
Definition AMReX_Arena.H:91
ArenaInfo & SetReadOnly() noexcept
Advise the runtime that the managed memory will be read-only on the device.
Definition AMReX_Arena.H:111
bool device_set_preferred
Advise the runtime to prefer the device for managed memory.
Definition AMReX_Arena.H:96
bool device_set_readonly
Advise the runtime that the managed memory is read-only on the device.
Definition AMReX_Arena.H:95
bool device_use_hostalloc
Use host-pinned memory (cudaMallocHost/hipHostMalloc).
Definition AMReX_Arena.H:97
ArenaInfo & SetReleaseThreshold(Long rt) noexcept
Set the usage threshold that triggers release of cached unused blocks before growing.
Definition AMReX_Arena.H:100
ArenaInfo & SetDefragmentation(bool b) noexcept
Enable or disable defragmentation in the arena.
Definition AMReX_Arena.H:138
Long release_threshold
When usage would exceed this, cached unused blocks are released first.
Definition AMReX_Arena.H:92
ArenaInfo & SetPreferred() noexcept
Advise the runtime to prefer device residence for the managed memory.
Definition AMReX_Arena.H:117
ArenaInfo & SetCpuMemory() noexcept
Configure the arena to use CPU (host) memory.
Definition AMReX_Arena.H:129
bool device_use_managed_memory
Use CUDA/HIP managed (unified) memory for GPU allocations.
Definition AMReX_Arena.H:94
bool use_cpu_memory
Allocate CPU (host) memory instead of GPU memory.
Definition AMReX_Arena.H:93
ArenaInfo & SetDeviceMemory() noexcept
Configure the arena to use non-managed GPU device memory.
Definition AMReX_Arena.H:105
bool defragmentation
Definition AMReX_Arena.H:98
ArenaInfo & SetHostAlloc() noexcept
Configure the arena to use host-pinned memory.
Definition AMReX_Arena.H:123
Definition AMReX_Arena.H:20