column_view.hpp
Go to the documentation of this file.
1 /*
2  * Copyright (c) 2019-2025, NVIDIA CORPORATION.
3  *
4  * Licensed under the Apache License, Version 2.0 (the "License");
5  * you may not use this file except in compliance with the License.
6  * You may obtain a copy of the License at
7  *
8  * http://www.apache.org/licenses/LICENSE-2.0
9  *
10  * Unless required by applicable law or agreed to in writing, software
11  * distributed under the License is distributed on an "AS IS" BASIS,
12  * WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied.
13  * See the License for the specific language governing permissions and
14  * limitations under the License.
15  */
16 #pragma once
17 
18 #include <cudf/types.hpp>
19 #include <cudf/utilities/error.hpp>
20 #include <cudf/utilities/prefetch.hpp>
21 #include <cudf/utilities/span.hpp>
24 
25 #include <limits>
26 #include <type_traits>
27 #include <vector>
28 
33 namespace CUDF_EXPORT cudf {
34 namespace detail {
54  public:
71  template <typename T = void,
72  CUDF_ENABLE_IF(std::is_same_v<T, void> or is_rep_layout_compatible<T>())>
73  T const* head() const noexcept
74  {
75  return static_cast<T const*>(get_data());
76  }
77 
90  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
91  T const* data() const noexcept
92  {
93  return head<T>() + _offset;
94  }
95 
106  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
107  T const* begin() const noexcept
108  {
109  return data<T>();
110  }
111 
122  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
123  T const* end() const noexcept
124  {
125  return begin<T>() + size();
126  }
127 
133  [[nodiscard]] size_type size() const noexcept { return _size; }
134 
140  [[nodiscard]] bool is_empty() const noexcept { return size() == 0; }
141 
147  [[nodiscard]] data_type type() const noexcept { return _type; }
148 
158  [[nodiscard]] bool nullable() const noexcept { return nullptr != _null_mask; }
159 
165  [[nodiscard]] size_type null_count() const { return _null_count; }
166 
182  [[nodiscard]] size_type null_count(
183  size_type begin,
184  size_type end,
186 
194  [[nodiscard]] bool has_nulls() const { return null_count() > 0; }
195 
209  [[nodiscard]] bool has_nulls(size_type begin,
210  size_type end,
212  {
213  return null_count(begin, end, stream) > 0;
214  }
215 
224  [[nodiscard]] bitmask_type const* null_mask() const noexcept { return _null_mask; }
225 
232  [[nodiscard]] size_type offset() const noexcept { return _offset; }
233 
234  protected:
244  [[nodiscard]] virtual void const* get_data() const noexcept { return _data; }
245 
246  data_type _type{type_id::EMPTY};
247  size_type _size{};
248  void const* _data{};
249  bitmask_type const* _null_mask{};
252  mutable size_type _null_count{};
253  size_type _offset{};
255 
256  column_view_base() = default;
257  virtual ~column_view_base() = default;
258  column_view_base(column_view_base const&) = default;
272 
298  size_type size,
299  void const* data,
300  bitmask_type const* null_mask,
302  size_type offset = 0);
303 };
304 
305 } // namespace detail
306 
328  public:
329  column_view() = default;
330 
331  // these pragmas work around the nvcc issue where if a column_view is used
332  // inside of a __device__ code path, these functions will end up being created
333  // as __host__ __device__ because they are explicitly defaulted. However, if
334  // they then end up being called by a simple __host__ function
335  // (eg std::vector destructor) you get a compile error because you're trying to
336  // call a __host__ __device__ function from a __host__ function.
337 #ifdef __CUDACC__
338 #pragma nv_exec_check_disable
339 #endif
340  ~column_view() override = default;
341 #ifdef __CUDACC__
342 #pragma nv_exec_check_disable
343 #endif
344  column_view(column_view const&) = default;
345  column_view(column_view&&) = default;
351  column_view& operator=(column_view const&) = default;
358 
386  size_type size,
387  void const* data,
388  bitmask_type const* null_mask,
390  size_type offset = 0,
391  std::vector<column_view> const& children = {});
392 
399  [[nodiscard]] column_view child(size_type child_index) const noexcept
400  {
401  return _children[child_index];
402  }
403 
409  [[nodiscard]] size_type num_children() const noexcept { return _children.size(); }
410 
416  auto child_begin() const noexcept { return _children.cbegin(); }
417 
423  auto child_end() const noexcept { return _children.cend(); }
424 
433  template <typename T, CUDF_ENABLE_IF(cudf::is_numeric<T>() or cudf::is_chrono<T>())>
434  column_view(device_span<T const> data)
435  : column_view(
436  cudf::data_type{cudf::type_to_id<T>()}, data.size(), data.data(), nullptr, 0, 0, {})
437  {
438  CUDF_EXPECTS(
439  data.size() <= static_cast<std::size_t>(std::numeric_limits<cudf::size_type>::max()),
440  "Data exceeds the column size limit",
441  std::overflow_error);
442  }
443 
455  template <typename T, CUDF_ENABLE_IF(cudf::is_numeric<T>() or cudf::is_chrono<T>())>
456  [[nodiscard]] operator device_span<T const>() const
457  {
458  CUDF_EXPECTS(type() == cudf::data_type{cudf::type_to_id<T>()},
459  "Device span type must match column view type.");
460  CUDF_EXPECTS(!nullable(), "A nullable column view cannot be converted to a device span.");
461  return device_span<T const>(data<T>(), size());
462  }
463 
464  protected:
474  void const* get_data() const noexcept override;
475 
476  private:
477  friend column_view bit_cast(column_view const& input, data_type type);
478 
479  std::vector<column_view> _children{};
481 }; // namespace cudf
482 
504  public:
505  mutable_column_view() = default;
506 
507  ~mutable_column_view() override{
508  // Needed so that the first instance of the implicit destructor for any TU isn't 'constructed'
509  // from a host+device function marking the implicit version also as host+device
510  };
511 
526 
553  size_type size,
554  void* data,
555  bitmask_type* null_mask,
557  size_type offset = 0,
558  std::vector<mutable_column_view> const& children = {});
559 
575  template <typename T = void,
576  CUDF_ENABLE_IF(std::is_same_v<T, void> or is_rep_layout_compatible<T>())>
577  T* head() const noexcept
578  {
579  return const_cast<T*>(detail::column_view_base::head<T>());
580  }
581 
594  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
595  T* data() const noexcept
596  {
597  return const_cast<T*>(detail::column_view_base::data<T>());
598  }
599 
610  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
611  T* begin() const noexcept
612  {
613  return const_cast<T*>(detail::column_view_base::begin<T>());
614  }
615 
626  template <typename T, CUDF_ENABLE_IF(is_rep_layout_compatible<T>())>
627  T* end() const noexcept
628  {
629  return const_cast<T*>(detail::column_view_base::end<T>());
630  }
631 
641  [[nodiscard]] bitmask_type* null_mask() const noexcept
642  {
643  return const_cast<bitmask_type*>(detail::column_view_base::null_mask());
644  }
645 
653  void set_null_count(size_type new_null_count);
654 
661  [[nodiscard]] mutable_column_view child(size_type child_index) const noexcept
662  {
663  return mutable_children[child_index];
664  }
665 
671  [[nodiscard]] size_type num_children() const noexcept { return mutable_children.size(); }
672 
678  auto child_begin() const noexcept { return mutable_children.begin(); }
679 
685  auto child_end() const noexcept { return mutable_children.end(); }
686 
692  operator column_view() const;
693 
694  protected:
704  [[nodiscard]] void const* get_data() const noexcept override;
705 
706  private:
708 
709  std::vector<mutable_column_view> mutable_children;
710 };
711 
719 
742 
765 
766 namespace detail {
782 std::size_t shallow_hash(column_view const& input);
783 
805 bool is_shallow_equivalent(column_view const& lhs, column_view const& rhs);
806 
807 } // namespace detail
808 } // 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:243
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:53
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.
T const * data() const noexcept
Returns the underlying data casted to the specified type, plus the offset.
Definition: column_view.hpp:91
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:73
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:178
int32_t size_type
Row index type for columns and tables.
Definition: types.hpp:95
uint32_t bitmask_type
Bitmask type stored as 32-bit unsigned integer.
Definition: types.hpp:96
constexpr CUDF_HOST_DEVICE bool is_chrono()
Indicates whether the type T is a chrono type.
Definition: traits.hpp:493
#define CUDF_ENABLE_IF(...)
Convenience macro for SFINAE as an unnamed template parameter.
Definition: traits.hpp:48
cuDF interfaces
Definition: host_udf.hpp:37
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:351
Defines the mapping between cudf::type_id runtime type information and concrete C++ types.
Type declarations for libcudf.