HIP runtime API reference reorganize

.wordlist.txt

@@ -32,6 +32,7 @@ enqueues
 entrypoint
 entrypoints
 enum
+enums
 embeded
 extern
 fatbinary

docs/doxygen/Doxyfile

@@ -829,8 +829,7 @@ WARN_LOGFILE           =
 # spaces. See also FILE_PATTERNS and EXTENSION_MAPPING
 # Note: If this tag is empty the current directory is searched.
 
-INPUT                  = mainpage.md \
-                         ../../include/hip \
+INPUT                  = ../../include/hip \
                          ../../../clr/hipamd/include/hip/amd_detail/amd_hip_gl_interop.h \
                          ../../../clr/hipamd/include/hip/amd_detail/amd_surface_functions.h \
                          ../../../clr/hipamd/include/hip/amd_detail/amd_hip_cooperative_groups.h \
@@ -2207,6 +2206,7 @@ PREDEFINED             = "__HIP_PLATFORM_AMD__" \
                          "__CG_QUALIFIER__=" \
                          "__CG_STATIC_QUALIFIER__=static" \
                          "_CG_STATIC_CONST_DECL_=static constexpr" \
+                         "HIP_PUBLIC_API" \
                          "HIP_ENABLE_WARP_SYNC_BUILTINS"
 
 # If the MACRO_EXPANSION and EXPAND_ONLY_PREDEF tags are set to YES then this

docs/index.md

@@ -54,15 +54,14 @@ On non-AMD platforms, like NVIDIA, HIP provides header files required to support
 
 :::{grid-item-card} Reference
 
-* {doc}`/doxygen/html/index`
+* [HIP runtime API](./reference/hip_runtime_api_reference)
+  * [Modules](./reference/hip_runtime_api/modules)
+  * [Global defines, enums, structs and files](./reference/hip_runtime_api/global_defines_enums_structs_files)
+* [HSA runtime API for ROCm](./reference/virtual_rocr)
 * [C++ language extensions](./reference/cpp_language_extensions)
 * [C++ language support](./reference/cpp_language_support)
 * [HIP math API](./reference/math_api)
 * [Comparing syntax for different APIs](./reference/terms)
-* [HSA runtime API for ROCm](./reference/virtual_rocr)
-* [HIP managed memory allocation API](./reference/unified_memory_reference)
-* [HIP virtual memory management API](./reference/virtual_memory_reference)
-* [HIP Cooperative groups API](./reference/cooperative_groups_reference)
 * [List of deprecated APIs](./reference/deprecated_api_list)
 * [FP8 numbers in HIP](./reference/fp8_numbers)
 

docs/reference/hip_runtime_api/global_defines_enums_structs_files.rst

@@ -0,0 +1,14 @@
+.. meta::
+  :description: The global defines, enum, structs and files reference page.
+
+.. _global_defines_enums_structs_files_reference:
+
+*******************************************************************************
+Global defines, enums, structs and files
+*******************************************************************************
+
+The structs, define macros, enums and files in the HIP runtime API.
+
+* :ref:`global_enum_defines_reference`
+* :doc:`hip:doxygen/html/annotated`
+* :doc:`hip:doxygen/html/files`

docs/reference/hip_runtime_api/global_defines_enums_structs_files/global_enum_and_defines.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The global enum and defines reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, global enum, defines
+
+.. _global_enum_defines_reference:
+
+*******************************************************************************
+Global enum and defines
+*******************************************************************************
+
+.. doxygengroup:: GlobalDefs
+   :content-only:

docs/reference/hip_runtime_api/modules.rst

@@ -0,0 +1,41 @@
+.. meta::
+  :description: The HIP runtime API modules reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, HIP runtime API modules, modules
+
+.. _modules_reference:
+
+*******************************************************************************
+Modules
+*******************************************************************************
+
+The API is organized into modules based on functionality.
+
+* :ref:`initialization_version_reference`
+* :ref:`device_management_reference`
+* :ref:`execution_control_reference`
+* :ref:`error_handling_reference`
+* :ref:`stream_management_reference`
+* :ref:`stream_memory_operations_reference`
+* :ref:`event_management_reference`
+* :ref:`memory_management_reference`
+
+  * :ref:`memory_management_deprecated_reference`
+  * :ref:`external_resource_interoperability_reference`
+  * :ref:`stream_ordered_memory_allocator_reference`
+  * :ref:`unified_memory_reference`
+  * :ref:`virtual_memory_reference`
+  * :ref:`texture_management_reference`
+  * :ref:`texture_management_deprecated_reference`
+  * :ref:`surface_object_reference`
+
+* :ref:`peer_to_peer_device_memory_access_reference`
+* :ref:`context_management_reference`
+* :ref:`module_management_reference`
+* :ref:`occupancy_reference`
+* :ref:`profiler_control_reference`
+* :ref:`launch_api_reference`
+* :ref:`runtime_compilation_reference`
+* :ref:`callback_activity_apis_reference`
+* :ref:`graph_management_reference`
+* :ref:`opengl_interoperability_reference`
+* :ref:`cooperative_groups_reference`

docs/reference/hip_runtime_api/modules/callback_activity_apis.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The callback activity APIs reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, callback activity APIs, callback activity
+
+.. _callback_activity_apis_reference:
+
+*******************************************************************************
+Callback activity APIs
+*******************************************************************************
+
+.. doxygengroup:: Callback
+   :content-only:

docs/reference/hip_runtime_api/modules/context_management.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The context management reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, context management, context
+
+.. _context_management_reference:
+
+*******************************************************************************
+Context management [deprecated]
+*******************************************************************************
+
+.. doxygengroup:: Context
+   :content-only:

docs/reference/cooperative_groups_reference.rst → docs/reference/hip_runtime_api/modules/cooperative_groups_reference.rst

@@ -1,11 +1,13 @@
 .. meta::
-  :description: This chapter lists types and device API wrappers related to the Cooperative Group feature. Programmers can directly use these API features in their kernels.
+  :description: This chapter lists types and device API wrappers related to the 
+                Cooperative Group feature. Programmers can directly use these 
+                API features in their kernels.
   :keywords: AMD, ROCm, HIP, cooperative groups
 
 .. _cooperative_groups_reference:
 
 *******************************************************************************
-HIP Cooperative groups API
+Cooperative groups
 *******************************************************************************
 
 Cooperative kernel launches

docs/reference/hip_runtime_api/modules/device_management.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The device management reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, device management, device
+
+.. _device_management_reference:
+
+*******************************************************************************
+Device management
+*******************************************************************************
+
+.. doxygengroup:: Device
+   :content-only:

docs/reference/hip_runtime_api/modules/error_handling.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The error handling reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, error handling, error
+
+.. _error_handling_reference:
+
+*******************************************************************************
+Error handling
+*******************************************************************************
+
+.. doxygengroup:: Error
+   :content-only:

docs/reference/hip_runtime_api/modules/event_management.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The event management reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, event management, event
+
+.. _event_management_reference:
+
+*******************************************************************************
+Event management
+*******************************************************************************
+
+.. doxygengroup:: Event
+   :content-only:

docs/reference/hip_runtime_api/modules/execution_control.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The execution control reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, execution control, execution
+
+.. _execution_control_reference:
+
+*******************************************************************************
+Execution control
+*******************************************************************************
+
+.. doxygengroup:: Execution
+   :content-only:

docs/reference/hip_runtime_api/modules/graph_management.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The graph management reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, graph management, graph
+
+.. _graph_management_reference:
+
+*******************************************************************************
+Graph management
+*******************************************************************************
+
+.. doxygengroup:: Graph
+   :content-only:

docs/reference/hip_runtime_api/modules/initialization_and_version.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The initialization and version reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, initialization, version
+
+.. _initialization_version_reference:
+
+*******************************************************************************
+Initialization and version
+*******************************************************************************
+
+.. doxygengroup:: Driver
+   :content-only:

docs/reference/hip_runtime_api/modules/launch_api.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The launch API reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, launch API, triple-chevron
+
+.. _launch_api_reference:
+
+*******************************************************************************
+Launch API
+*******************************************************************************
+
+.. doxygengroup:: Clang
+   :content-only:

docs/reference/hip_runtime_api/modules/memory_management.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The memory management reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, memory management, memory
+
+.. _memory_management_reference:
+
+*******************************************************************************
+Memory management
+*******************************************************************************
+
+.. doxygengroup:: Memory
+   :content-only:

docs/reference/hip_runtime_api/modules/memory_management/external_resource_interoperability.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The external resource interoperability reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, external resource interoperability
+
+.. _external_resource_interoperability_reference:
+
+*******************************************************************************
+External resource interoperability
+*******************************************************************************
+
+.. doxygengroup:: External
+   :content-only:

docs/reference/hip_runtime_api/modules/memory_management/memory_management_deprecated.rst

@@ -0,0 +1,11 @@
+.. meta::
+  :description: The deprecated memory management reference page.
+
+.. _memory_management_deprecated_reference:
+
+*******************************************************************************
+Memory management (deprecated)
+*******************************************************************************
+
+.. doxygengroup:: MemoryD
+   :content-only:

docs/reference/hip_runtime_api/modules/memory_management/stream_ordered_memory_allocator.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The stream ordered memory allocator reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, stream ordered memory allocator
+
+.. _stream_ordered_memory_allocator_reference:
+
+*******************************************************************************
+Stream ordered memory allocator
+*******************************************************************************
+
+.. doxygengroup:: StreamO
+   :content-only:

docs/reference/hip_runtime_api/modules/memory_management/surface_object.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The surface object reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, surface object, surface
+
+.. _surface_object_reference:
+
+*******************************************************************************
+Surface object
+*******************************************************************************
+
+.. doxygengroup:: Surface
+   :content-only:

docs/reference/hip_runtime_api/modules/memory_management/texture_management.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The texture management reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, texture management, texture
+
+.. _texture_management_reference:
+
+*******************************************************************************
+Texture management
+*******************************************************************************
+
+.. doxygengroup:: Texture
+   :content-only:

docs/reference/hip_runtime_api/modules/memory_management/texture_management_deprecated.rst

@@ -0,0 +1,12 @@
+.. meta::
+  :description: The deprecated texture management reference page.
+  :keywords: AMD, ROCm, HIP, CUDA, deprecated texture management
+
+.. _texture_management_deprecated_reference:
+
+*******************************************************************************
+Texture management (deprecated)
+*******************************************************************************
+
+.. doxygengroup:: TextureD
+   :content-only:

docs/reference/unified_memory_reference.rst → docs/reference/hip_runtime_api/modules/memory_management/unified_memory_reference.rst

@@ -1,12 +1,11 @@
 .. meta::
-  :description: This chapter describes introduces Unified Memory (UM) and shows
-                how to use it in AMD HIP.
+  :description: The managed memory reference page.
   :keywords: AMD, ROCm, HIP, CUDA, unified memory, unified, memory, UM, APU
 
 .. _unified_memory_reference:
 
 *******************************************************************************
-HIP managed memory allocation API
+Managed memory
 *******************************************************************************
 
 .. doxygengroup:: MemoryM