Changelog

libcu++ 1.9.0

Adds float and double support to cuda::std::atomic and cuda::atomic. This release also adds workflows for contributors based on Docker to improve testing and coverage.

Supported ABI Versions: 4 (default), 3, and 2.

New Features

• #286: Add atomics for floating point types.
  • Thanks Daniel Jünger for this contribution.
• #284: cuda::proclaim_return_type for use with extended lambda support in NVCC.
• #267: Docker refactor, parameterizes OS and compiler versions.

Issues Fixed

• #280: NVHPC: Disable <nv/target> macro code paths when compiled without -stdpar.
• #282: Prevent usage of cuda::atomic::fetch_max/min for non-integral types.
• #288: Fix shortcut in fetch_min CAS loop.
  • Thanks Daniel Jünger for this contribution.
• #291: Remove usage of find_path to locate cuda/std/detail/__config.
  • Thanks Robert Maynard for this contribution.
• #276: Delete tests for unsupported header <compare>.
• #293: Fix failures in several tests unsupportable by NVRTC.
• #303: Move the emission of atomic errors on unsupported platforms to <atomic>.
• #305: Add workflow to add issues/PRs to Project.
• #314: Remove SM_35 from testing.
• #312: Use escape hook for removal of <ciso646>.
• #310: <atomics> Remove defaulted copy constructor from __cxx_atomic_lock_impl.
• #300: Soundness bugfix for barrier<thread_scope_block> on sm_70.
• #319: Fix ubuntu18 failing in CI due to missing lit prereqs.
• #318: Fix gcc12 issues.
• #320: Use cache_from to speed up builds if local versions exist.
• #304: Fix <chrono> and <atomic> build errors with clang-cuda.
• #324: Also disable tests on windows && pre-sm-70.

libcu++ 1.8.1

libcu++ 1.8.1 is a minor release. It fixes minor issues in source, tests, and documentation.

Supported ABI Versions: 4 (default), 3, and 2.

Issues Fixed

• #268: Remove NVIDIA internal paths from CMake includes.
• #265: Move pipeline into libcudacxx. Previously was a seperate CTK component.
• #264: Fix builds using NVHPC by adding a new line.
  • Thanks Chengjie Wang and Royil Damer for this contribution.
• #261: Fix extra line in perform_tests.bash causing invalid test results.
  • Thanks Chengjie Wang and Royil Damer for this contribution.
• #246: Documentation fixes regarding atomics in GPU memory.
  • Thanks Daniel Lustig for this contribution.
• #258: Lock contrast of our documenation’s search text field.
  • Thanks Bradley Dice for this contribution.
• #259: Add system_header pragma to portions of <nv/target>
• #249: Documentation update for building libcudacxx.
• #247: Update godbolt links in examples.
  • Thanks Asher Mancinelli for this contribution.

libcu++ 1.8.0

libcu++ 1.8.0 is a major release. It adds several constexpr bit manipulation functions from C++20’s <bit> to C++11 and up. Also added is cuda::std::array providing fixed size arrays and iterators for both host and device code.

Supported ABI Versions: 4 (default), 3, and 2.

New Features

• #237: Add <cuda/std/bit> and enable backports to C++11.
• #243: Add <cuda/std/array> and <cuda/std/iterator>.

Issues Fixed

• #234: Fix building with GCC/Clang when NVCC was not being used.
• #240: Create a config for lit to generate a JSON output of the build status.
  • Thanks Royil Damer for this contribution.
• #241: Fix octal notation of libcudacxx version number.
• #242: Add support for find_package and add_subdirectory in CMake.
• #244: Merge build system improvements from NVC++ branch.
• #250: Fix pragma typo on MSVC.
• #251: Add several new compilers versions to our docker suite.
• #252: Fix several deprecations in Clang 13.
• #253: Fix truncations and warnings in numerics.
• #254: Fix warnings in <array> tests and move __cuda_std__ escapes in <algorithm>
• #255: Fix deprecated copy ctor warnings in __annotated_ptr for Clang 13.
• #256: Fix SM detection in the perform_tests script.

libcu++ 1.7.0

libcu++ 1.7.0 is a major release. It adds cuda::std::atomic_ref for integral types. cuda::std::atomic_ref may potentially replace uses of CUDA specific atomicOperator(_Scope) calls and provides a singular API for host and device code.

Supported ABI Versions: 4 (default), 3, and 2.

New Features

• #203 Implements cuda::std::atomic_ref for integral types.

Issues Fixed

• #204: Fallback macro backend in <nv/target> when C or pre-C++11 dialects are used.
• #206: Fix compilation with ASAN enabled.
  • Thanks Janusz Lisiecki for this contribution.
• #207: Fix compilation of <cuda/std/atomic> for GCC/Clang.
• #208: Flip an internal directory symlink, fixes packaging issues for internal tools.
• #212: Fix <nv/target> on MSVC, fallback macros would always choose pre-C++11 backend.
• #216: Annotated Pointer documentation.
  • Thanks Gonzalo Brito for this contribution.
• #215: Add SM87 awareness to <nv/target>.
• #217: Fix how CUDACC version is calculated for __int128 support.
• #228: Fix LLVM lit pattern matching in test score calculation.
• #227: Silence 4296 for type_traits.
• #225: Fix calculation of _LIBCUDACXX_CUDACC_VER broken from #217.
  • Thanks Robert Maynard for this contribution.
• #220: memcpy_async should cache only in L2 when possible.
• #219: Change atomic/atomic_ref ctors to prevent copy construction.

libcu++ 1.6.0 (CUDA Toolkit 11.5)

libcu++ 1.6.0 is a major release. It changes the default alignment of cuda::std::complex for better code generation and changes cuda::std::atomic to use <nv/target> as the primary dispatch mechanism.

This release adds cuda::annotated_ptr and cuda::access_property, two APIs that allow associating an address space and an explicit caching policy with a pointer, and the related cuda::apply_access_property, cuda::associate_access_property and cuda::discard_memory APIs.

This release introduces ABI version 4, which is now the default.

Supported ABI Versions: 4 (default), 3, and 2.

Included in: CUDA Toolkit 11.5.

Issues Fixed

• #197: Rework cuda::atomic::fetch_max/min so that it is RMW and actually works.
• #196: Fix missing path host atomic path for NVC++.
• #195: Fix missing inline specifier on internal atomic functions.
• #194: <cuda/std/barrier> and <cuda/std/atomic> failed to compile with NVRTC.
• #179: Refactors the atomic layer to allow for layering the host device/host abstractions.
• #189: Changed pragmas for silencing chrono long double warnings.
• #186: Allows <nv/target> to be used under NVRTC.
• #177: Allows <nv/target> to build when compiled under C and C++98.
  • Thanks to David Olsen for this contribution.
• #172: Introduces ABI version 4.
  • Forces cuda::std::complex alignment for enhanced performance.
  • Sets the internal representation of cuda::std::chrono literals to double.
• #165: For tests on some older distributions keep using Python 3, but downgrade lit.
• #164: Fixes testing issues related to Python 2/3 switch for lit.
  • Thanks to Royil Damer for this contribution.

libcu++ 1.5.0 (CUDA Toolkit 11.4)

libcu++ 1.5.0 is a major release. It adds <nv/target>, the library support header for the new if target target specialization mechanism.

Supported ABI Versions: 3 (default) and 2.

Included in: CUDA Toolkit 11.4.

New Features

• <nv/target> - Portability macros for NVCC/NVC++ and other compilers.

Issues Fixed

• Documentation: Several typo fixes.
• #126: Compiler warnings in <cuda/atomic>.
  • Thanks to anstellaire for this contribution.

libcu++ 1.4.1 (CUDA Toolkit 11.3)

libcu++ 1.4.1 is a minor bugfix release.

Supported ABI versions: 3 (default) and 2.

Included in: CUDA Toolkit 11.3.

Other Enhancements

• Documentation: Several enhancements and fixed a few broken links.
• #108: Added constexpr to synchronization object constructors.
  • Thanks to Olivier Giroux for this contribution.

Issues Fixed

• #106: Fixed host code atomics on VS 2019 Version 16.5 / MSVC 1925 and above.
• #101: Fixed cuda::std::complex for NVRTC.
• #118: Renamed __is_convertible, which NVCC treats as a context sensitive keyword.

libcu++ 1.4.0

libcu++ 1.4.0 adds <cuda/std/complex>, NVCC + MSVC support for <cuda/std/tuple>, and backports of C++20 <cuda/std/chrono> and C++17 <cuda/std/type_traits> features to C++14.

Supported ABI versions: 3 (default) and 2.

New Features

• #32: <cuda/std/complex>.
  • long double is not supported and disabled when building with NVCC.
• #34: C++17/20 <cuda/std/chrono> backported to C++14.
  • Thanks to Jake Hemstad and Paul Taylor for this contribution.
• #44: C++17 <cuda/std/type_traits> backported to C++14.
  • Thanks to Jake Hemstad and Paul Taylor for this contribution.
• #66: C++17 cuda::std::byte (in <cuda/std/cstddef>) backported to C++14.
  • Thanks to Jake Hemstad and Paul Taylor for this contribution.
• #76: C++20 cuda::std::is_constant_evaluated backported to C++11.
  • Thanks to Jake Hemstad and Paul Taylor for this contribution.

Other Enhancements

• Documentation has been improved and reorganized.
• #43: Atomics on MSVC have been decoupled from host Standard Library.
• #78: Fixed header licensing.
• #31: Revamped examples and benchmarks.
  • Thanks to Jake Hemstad for this contribution.

Issues Fixed

• #53, #80, #81: Improved documentation for <cuda/pipeline> and the asynchronous operations API.
• #14: NVRTC missing definitions for several macros.
  • Thanks to Ben Barsdell for this contribution.
• #56: <cuda/std/tuple> now works on a set of most recent MSVC compilers.
• #66, #82: <cuda/std/chrono>/<cuda/std/type_traits> backports.
  • Thanks to Jake Hemstad and Paul Taylor for this contribution.

libcu++ 1.3.0 (CUDA Toolkit 11.2)

libcu++ 1.3.0 adds <cuda/std/tuple> and cuda::std::pair, although they are not supported with NVCC + MSVC. It also adds documentation.

Supported ABI versions: 3 (default) and 2.

Included in: CUDA Toolkit 11.2.

New Features

• #17: <cuda/std/tuple>: cuda::std::tuple, a fixed-size collection of heterogeneous values. Not supported with NVCC + MSVC.
• #17: <cuda/std/utility>: cuda::std::pair, a collection of two heterogeneous values. The only <cuda/std/utility> facilities supported are cuda::std::pair. Not supported with NVCC + MSVC.

Other Enhancements

• Documentation.

Issues Fixed

• #21: Disable __builtin_is_constant_evaluated usage with NVCC in C++11 mode because it’s broken.
• #25: Fix some declarations/definitions in __threading_support which have inconsistent qualifiers. Thanks to Gonzalo Brito Gadeschi for this contribution.

libcu++ 1.2.0 (CUDA Toolkit 11.1)

libcu++ 1.2.0 adds <cuda/pipeline>/cuda::pipeline, a facility for coordinating cuda::memcpy_async operations. This release introduces ABI version 3, which is now the default.

Supported ABI versions: 3 (default) and 2.

Included in: CUDA Toolkit 11.1.

ABI Breaking Changes

• ABI version 3 has been introduced and is now the default. A new ABI version was necessary to improve the performance of cuda::[std::]barrier by changing its alignment. Users may define _LIBCUDACXX_CUDA_ABI_VERSION=2 before including any libcu++ or CUDA headers to use ABI version 2, which was the default for the 1.1.0 / CUDA 11.0 release. Both ABI version 3 and ABI version 2 will be supported until the next major CUDA release.

New Features

• <cuda/pipeline>: cuda::pipeline, a facility for coordinating cuda::memcpy_async operations.
• <cuda/std/version>: API version macros _LIBCUDACXX_CUDA_API_VERSION, _LIBCUDACXX_CUDA_API_VERSION_MAJOR, _LIBCUDACXX_CUDA_API_VERSION_MINOR, and _LIBCUDACXX_CUDA_API_VERSION_PATCH.
• ABI version switching: users can define _LIBCUDACXX_CUDA_ABI_VERSION to request a particular supported ABI version. _LIBCUDACXX_CUDA_ABI_VERSION_LATEST is set to the latest ABI version, which is always the default.

Other Enhancements

• <cuda/latch>/<cuda/semaphore>: <cuda/*> headers added for cuda::latch, cuda::counting_semaphore, and cuda::binary_semaphore. These features were available in prior releases, but you had to include <cuda/std/latch> and <cuda/std/semaphore> to access them.
• NVCC + GCC 10 support.
• NVCC + Clang 10 support.

libcu++ 1.1.0 (CUDA Toolkit 11.0)

libcu++ 1.1.0 introduces the world’s first implementation of the Standard C++20 synchronization library: <cuda/[std/]barrier>, <cuda/std/latch>, <cuda/std/semaphore>, cuda::[std::]atomic_flag::test, cuda::[std::]atomic::wait, and cuda::[std::]atomic::notify*. An extension for managing asynchronous local copies, cuda::memcpy_async is introduced as well. It also adds <cuda/std/chrono>, <cuda/std/ratio>, and most of <cuda/std/functional>.

Supported ABI versions: 2.

Included in: CUDA Toolkit 11.0.

ABI Breaking Changes

• ABI version 2 has been introduced and is now the default. A new ABI version was introduced because it is our policy to do so in every major CUDA toolkit release. ABI version 1 is no longer supported.

API Breaking Changes

• Atomics on Pascal + Windows are disabled because the platform does not support them and on this platform the CUDA driver rejects binaries containing these operations.

New Features

• <cuda/[std/]barrier>: C++20’s cuda::[std::]barrier, an asynchronous thread coordination mechanism whose lifetime consists of a sequence of barrier phases, where each phase allows at most an expected number of threads to block until the expected number of threads arrive at the barrier. It is backported to C++11. The cuda::barrier variant takes an additional cuda::thread_scope parameter.
• <cuda/barrier>: cuda::memcpy_async, asynchronous local copies. This facility is NOT for transferring data between threads or transferring data between host and device; it is not a cudaMemcpyAsync replacement or abstraction. It uses cuda::[std::]barriers objects to synchronize the copies.
• <cuda/std/functional>: common function objects, such as cuda::std::plus, cuda::std::minus, etc. cuda::std::function, cuda::std::bind, cuda::std::hash, and cuda::std::reference_wrapper are omitted.

Other Enhancements

• Upgraded to a newer version of upstream libc++.
• Standalone NVRTC support.
• C++17 support.
• NVCC + GCC 9 support.
• NVCC + Clang 9 support.
• Build with warnings-as-errors.

Issues Fixed

• Made __cuda_memcmp inline to fix ODR violations when compiling multiple translation units.

libcu++ 1.0.0 (CUDA Toolkit 10.2)

libcu++ 1.0.0 is the first release of libcu++, the C++ Standard Library for your entire system. It brings C++ atomics to CUDA: <cuda/[std/]atomic>. It also introduces <cuda/std/type_traits>, <cuda/std/cassert>, <cuda/std/cfloat>, <cuda/std/cstddef>, and <cuda/std/cstdint>.

Supported ABI versions: 1.

Included in: CUDA Toolkit 10.2.

New Features

• <cuda/[std/]atomic>:
  • cuda::thread_scope: An enumeration that specifies which group of threads can synchronize with each other using a concurrency primitive.
  • cuda::atomic<T, Scope>: Scoped atomic objects.
  • cuda::std::atomic<T>: Atomic objects.
• <cuda/std/type_traits>: Type traits and metaprogramming facilities.
• <cuda/std/cassert>: assert, an error-reporting mechanism.
• <cuda/std/cstddef>: Builtin fundamental types.
• <cuda/std/cstdint>: Builtin integral types.
• <cuda/std/cfloat>: Builtin floating point types.

Known Issues

• Due to circumstances beyond our control, the NVIDIA-provided Debian packages install libcu++ to the wrong path. This makes libcu++ unusable if installed from the NVIDIA-provided Debian packages and may interfere with the operation of your host C++ Standard Library.