column_view.hpp
Go to the documentation of this file.
1 /*
2  * SPDX-FileCopyrightText: Copyright (c) 2019-2025, NVIDIA CORPORATION.
3  * SPDX-License-Identifier: Apache-2.0
4  */
5 #pragma once
6 
7 #include <cudf/types.hpp>
10 #include <cudf/utilities/span.hpp>
13 
14 #include <limits>
15 #include <type_traits>
16 #include <vector>
17 
22 namespace CUDF_EXPORT cudf {
23 namespace detail {
43  public:
60  template <typename T = void,
61  CUDF_ENABLE_IF(std::is_same_v<T, void> or is_rep_layout_compatible<T>())>
62  T const* head() const noexcept
63  {
64  return static_cast<T const*>(get_data());
65  }
66 
79  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
80  T const* data() const noexcept
81  {
82  return head<T>() + _offset;
83  }
84 
95  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
96  T const* begin() const noexcept
97  {
98  return data<T>();
99  }
100 
111  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
112  T const* end() const noexcept
113  {
114  return begin<T>() + size();
115  }
116 
122  [[nodiscard]] size_type size() const noexcept { return _size; }
123 
129  [[nodiscard]] bool is_empty() const noexcept { return size() == 0; }
130 
136  [[nodiscard]] data_type type() const noexcept { return _type; }
137 
147  [[nodiscard]] bool nullable() const noexcept { return nullptr != _null_mask; }
148 
154  [[nodiscard]] size_type null_count() const { return _null_count; }
155 
171  [[nodiscard]] size_type null_count(
172  size_type begin,
173  size_type end,
175 
183  [[nodiscard]] bool has_nulls() const { return null_count() > 0; }
184 
198  [[nodiscard]] bool has_nulls(size_type begin,
199  size_type end,
201  {
202  return null_count(begin, end, stream) > 0;
203  }
204 
213  [[nodiscard]] bitmask_type const* null_mask() const noexcept { return _null_mask; }
214 
221  [[nodiscard]] size_type offset() const noexcept { return _offset; }
222 
223  protected:
233  [[nodiscard]] virtual void const* get_data() const noexcept { return _data; }
234 
235  data_type _type{type_id::EMPTY};
236  size_type _size{};
237  void const* _data{};
238  bitmask_type const* _null_mask{};
241  mutable size_type _null_count{};
242  size_type _offset{};
244 
245  column_view_base() = default;
246  virtual ~column_view_base() = default;
247  column_view_base(column_view_base const&) = default;
261 
287  size_type size,
288  void const* data,
289  bitmask_type const* null_mask,
291  size_type offset = 0);
292 };
293 
294 } // namespace detail
295 
317  public:
318  column_view() = default;
319 
320  // these pragmas work around the nvcc issue where if a column_view is used
321  // inside of a __device__ code path, these functions will end up being created
322  // as __host__ __device__ because they are explicitly defaulted. However, if
323  // they then end up being called by a simple __host__ function
324  // (eg std::vector destructor) you get a compile error because you're trying to
325  // call a __host__ __device__ function from a __host__ function.
326 #ifdef __CUDACC__
327 #pragma nv_exec_check_disable
328 #endif
329  ~column_view() override = default;
330 #ifdef __CUDACC__
331 #pragma nv_exec_check_disable
332 #endif
333  column_view(column_view const&) = default;
334  column_view(column_view&&) = default;
340  column_view& operator=(column_view const&) = default;
347 
375  size_type size,
376  void const* data,
377  bitmask_type const* null_mask,
379  size_type offset = 0,
380  std::vector<column_view> const& children = {});
381 
388  [[nodiscard]] column_view child(size_type child_index) const noexcept
389  {
390  return _children[child_index];
391  }
392 
398  [[nodiscard]] size_type num_children() const noexcept { return _children.size(); }
399 
405  auto child_begin() const noexcept { return _children.cbegin(); }
406 
412  auto child_end() const noexcept { return _children.cend(); }
413 
422  template <typename T, CUDF_ENABLE_IF(cudf::is_numeric<T>() or cudf::is_chrono<T>())>
423  column_view(device_span<T const> data)
424  : column_view(
425  cudf::data_type{cudf::type_to_id<T>()}, data.size(), data.data(), nullptr, 0, 0, {})
426  {
427  CUDF_EXPECTS(
428  data.size() <= static_cast<std::size_t>(std::numeric_limits<cudf::size_type>::max()),
429  "Data exceeds the column size limit",
430  std::overflow_error);
431  }
432 
444  template <typename T, CUDF_ENABLE_IF(cudf::is_numeric<T>() or cudf::is_chrono<T>())>
445  [[nodiscard]] operator device_span<T const>() const
446  {
447  CUDF_EXPECTS(type() == cudf::data_type{cudf::type_to_id<T>()},
448  "Device span type must match column view type.");
449  CUDF_EXPECTS(!nullable(), "A nullable column view cannot be converted to a device span.");
450  return device_span<T const>(data<T>(), size());
451  }
452 
453  protected:
463  void const* get_data() const noexcept override;
464 
465  private:
466  friend column_view bit_cast(column_view const& input, data_type type);
467 
468  std::vector<column_view> _children{};
470 }; // namespace cudf
471 
493  public:
494  mutable_column_view() = default;
495 
496  ~mutable_column_view() override {
497  // Needed so that the first instance of the implicit destructor for any TU isn't 'constructed'
498  // from a host+device function marking the implicit version also as host+device
499  };
500 
515 
542  size_type size,
543  void* data,
544  bitmask_type* null_mask,
546  size_type offset = 0,
547  std::vector<mutable_column_view> const& children = {});
548 
564  template <typename T = void,
565  CUDF_ENABLE_IF(std::is_same_v<T, void> or is_rep_layout_compatible<T>())>
566  T* head() const noexcept
567  {
568  return const_cast<T*>(detail::column_view_base::head<T>());
569  }
570 
583  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
584  T* data() const noexcept
585  {
586  return const_cast<T*>(detail::column_view_base::data<T>());
587  }
588 
599  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
600  T* begin() const noexcept
601  {
602  return const_cast<T*>(detail::column_view_base::begin<T>());
603  }
604 
615  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
616  T* end() const noexcept
617  {
618  return const_cast<T*>(detail::column_view_base::end<T>());
619  }
620 
630  [[nodiscard]] bitmask_type* null_mask() const noexcept
631  {
632  return const_cast<bitmask_type*>(detail::column_view_base::null_mask());
633  }
634 
642  void set_null_count(size_type new_null_count);
643 
650  [[nodiscard]] mutable_column_view child(size_type child_index) const noexcept
651  {
652  return mutable_children[child_index];
653  }
654 
660  [[nodiscard]] size_type num_children() const noexcept { return mutable_children.size(); }
661 
667  auto child_begin() const noexcept { return mutable_children.begin(); }
668 
674  auto child_end() const noexcept { return mutable_children.end(); }
675 
681  operator column_view() const;
682 
683  protected:
693  [[nodiscard]] void const* get_data() const noexcept override;
694 
695  private:
697 
698  std::vector<mutable_column_view> mutable_children;
699 };
700 
708 
731 
754 
755 namespace detail {
771 std::size_t shallow_hash(column_view const& input);
772 
794 bool is_shallow_equivalent(column_view const& lhs, column_view const& rhs);
795 
796 } // namespace detail
797 } // namespace CUDF_EXPORT cudf
A non-owning, immutable view of device data as a column of elements, some of which may be null as ind...
column_view(column_view &&)=default
Move constructor.
size_type num_children() const noexcept
Returns the number of child columns.
auto child_begin() const noexcept
Returns iterator to the beginning of the ordered sequence of child column-views.
column_view & operator=(column_view &&)=default
Move assignment operator.
column_view & operator=(column_view const &)=default
Copy assignment operator.
void const * get_data() const noexcept override
Returns pointer to the base device memory allocation.
auto child_end() const noexcept
Returns iterator to the end of the ordered sequence of child column-views.
column_view child(size_type child_index) const noexcept
Returns the specified child.
column_view(data_type type, size_type size, void const *data, bitmask_type const *null_mask, size_type null_count, size_type offset=0, std::vector< column_view > const &children={})
Construct a column_view from pointers to device memory for the elements and bitmask of the column.
column_view(column_view const &)=default
Copy constructor.
Indicator for the logical data type of an element in a column.
Definition: types.hpp:238
A non-owning, immutable view of device data as a column of elements, some of which may be null as ind...
Definition: column_view.hpp:42
T const * end() const noexcept
Return one past the last element after underlying data is casted to the specified type.
data_type type() const noexcept
Returns the element data_type
bool has_nulls(size_type begin, size_type end, rmm::cuda_stream_view stream=cudf::get_default_stream()) const
Indicates if the column contains null elements in the range [begin, end), i.e., null_count(begin,...
column_view_base(column_view_base &&)=default
Move constructor.
column_view_base(data_type type, size_type size, void const *data, bitmask_type const *null_mask, size_type null_count, size_type offset=0)
Construct a column_view_base from pointers to device memory for the elements and bitmask of the colum...
size_type null_count() const
Returns the count of null elements.
size_type null_count(size_type begin, size_type end, rmm::cuda_stream_view stream=cudf::get_default_stream()) const
Returns the count of null elements in the range [begin, end)
column_view_base & operator=(column_view_base const &)=default
Copy assignment operator.
column_view_base & operator=(column_view_base &&)=default
Move assignment operator.
size_type size() const noexcept
Returns the number of elements in the column.
T const * begin() const noexcept
Return first element (accounting for offset) after underlying data is casted to the specified type.
Definition: column_view.hpp:96
T const * data() const noexcept
Returns the underlying data casted to the specified type, plus the offset.
Definition: column_view.hpp:80
size_type offset() const noexcept
Returns the index of the first element relative to the base memory allocation, i.e....
virtual void const * get_data() const noexcept
Returns pointer to the base device memory allocation.
T const * head() const noexcept
Returns pointer to the base device memory allocation casted to the specified type.
Definition: column_view.hpp:62
bool has_nulls() const
Indicates if the column contains null elements, i.e., null_count() > 0
bitmask_type const * null_mask() const noexcept
Returns raw pointer to the underlying bitmask allocation.
bool nullable() const noexcept
Indicates if the column can contain null elements, i.e., if it has an allocated bitmask.
column_view_base(column_view_base const &)=default
Copy constructor.
bool is_empty() const noexcept
Returns true if size() returns zero, or false otherwise.
A non-owning, mutable view of device data as a column of elements, some of which may be null as indic...
T * head() const noexcept
Returns pointer to the base device memory allocation casted to the specified type.
size_type num_children() const noexcept
Returns the number of child columns.
T * begin() const noexcept
Return first element (accounting for offset) after underlying data is casted to the specified type.
void set_null_count(size_type new_null_count)
Set the null count.
auto child_begin() const noexcept
Returns iterator to the beginning of the ordered sequence of child column-views.
mutable_column_view(data_type type, size_type size, void *data, bitmask_type *null_mask, size_type null_count, size_type offset=0, std::vector< mutable_column_view > const &children={})
Construct a mutable_column_view from pointers to device memory for the elements and bitmask of the co...
T * data() const noexcept
Returns the underlying data casted to the specified type, plus the offset.
mutable_column_view(mutable_column_view const &)=default
Copy constructor.
mutable_column_view & operator=(mutable_column_view &&)=default
Move assignment operator.
mutable_column_view & operator=(mutable_column_view const &)=default
Copy assignment operator.
auto child_end() const noexcept
Returns iterator to the end of the ordered sequence of child column-views.
bitmask_type * null_mask() const noexcept
Returns raw pointer to the underlying bitmask allocation.
void const * get_data() const noexcept override
Returns pointer to the base device memory allocation.
mutable_column_view child(size_type child_index) const noexcept
Returns a reference to the specified child.
mutable_column_view(mutable_column_view &&)=default
Move constructor.
T * end() const noexcept
Return one past the last element after underlying data is casted to the specified type.
std::size_t shallow_hash(column_view const &input)
Computes a hash value from the shallow state of the specified column.
bool is_shallow_equivalent(column_view const &lhs, column_view const &rhs)
Uses only shallow state to determine if two column_views view equivalent columns.
cudf::size_type null_count(bitmask_type const *bitmask, size_type start, size_type stop, rmm::cuda_stream_view stream=cudf::get_default_stream())
Given a validity bitmask, counts the number of null elements (unset bits) in the range [start,...
rmm::cuda_stream_view const get_default_stream()
Get the current default stream.
#define CUDF_EXPECTS(...)
Macro for checking (pre-)conditions that throws an exception when a condition is violated.
Definition: error.hpp:143
int32_t size_type
Row index type for columns and tables.
Definition: types.hpp:84
uint32_t bitmask_type
Bitmask type stored as 32-bit unsigned integer.
Definition: types.hpp:85
constexpr CUDF_HOST_DEVICE bool is_chrono()
Indicates whether the type T is a chrono type.
Definition: traits.hpp:490
#define CUDF_ENABLE_IF(...)
Convenience macro for SFINAE as an unnamed template parameter.
Definition: traits.hpp:39
cuDF interfaces
Definition: host_udf.hpp:26
bool nullable(table_view const &view)
Returns True if any of the columns in the table is nullable. (not entire hierarchy)
mutable_column_view bit_cast(mutable_column_view const &input, data_type type)
Zero-copy cast between types with the same size and compatible underlying representations.
size_type count_descendants(column_view parent)
Counts the number of descendants of the specified parent.
APIs for spans.
Device version of C++20 std::span with reduced feature set.
Definition: span.hpp:323
Defines the mapping between cudf::type_id runtime type information and concrete C++ types.
Type declarations for libcudf.