diff --git a/src/main/cpp/benchmarks/common/generate_input.cu b/src/main/cpp/benchmarks/common/generate_input.cu index 3b1376c89a..75f0a8fca0 100644 --- a/src/main/cpp/benchmarks/common/generate_input.cu +++ b/src/main/cpp/benchmarks/common/generate_input.cu @@ -520,7 +520,7 @@ std::unique_ptr create_random_utf8_string_column(data_profile cons return cudf::make_strings_column( num_rows, std::move(offsets), - std::move(chars), + std::move(chars->release().data.release()[0]), profile.get_null_frequency().has_value() ? std::move(result_bitmask) : rmm::device_buffer{}, null_count); } diff --git a/src/main/cpp/src/cast_decimal_to_string.cu b/src/main/cpp/src/cast_decimal_to_string.cu index 0cd2713a2f..01fc5c5a92 100644 --- a/src/main/cpp/src/cast_decimal_to_string.cu +++ b/src/main/cpp/src/cast_decimal_to_string.cu @@ -191,7 +191,7 @@ struct dispatch_decimal_to_non_ansi_string_fn { return make_strings_column(input.size(), std::move(offsets), - std::move(chars), + std::move(chars->release().data.release()[0]), input.null_count(), cudf::detail::copy_bitmask(input, stream, mr)); } diff --git a/src/main/cpp/src/cast_float_to_string.cu b/src/main/cpp/src/cast_float_to_string.cu index 6fc4d20f79..c0e0875914 100644 --- a/src/main/cpp/src/cast_float_to_string.cu +++ b/src/main/cpp/src/cast_float_to_string.cu @@ -88,7 +88,7 @@ struct dispatch_float_to_string_fn { return make_strings_column(strings_count, std::move(offsets), - std::move(chars), + std::move(chars->release().data.release()[0]), floats.null_count(), cudf::detail::copy_bitmask(floats, stream, mr)); } diff --git a/src/main/cpp/src/cast_string.cu b/src/main/cpp/src/cast_string.cu index 59a27a59b7..c2a8190062 100644 --- a/src/main/cpp/src/cast_string.cu +++ b/src/main/cpp/src/cast_string.cu @@ -624,7 +624,7 @@ void validate_ansi_column(column_view const& col, dest.resize(string_bounds[1] - string_bounds[0]); cudaMemcpyAsync(dest.data(), - &source_col.chars().data()[string_bounds[0]], + &source_col.chars_begin(stream)[string_bounds[0]], string_bounds[1] - string_bounds[0], cudaMemcpyDeviceToHost, stream.value()); @@ -667,7 +667,7 @@ struct string_to_integer_impl { detail::string_to_integer_kernel<<>>( data.data(), null_mask.data(), - string_col.chars().data(), + string_col.chars_begin(stream), string_col.offsets().data(), string_col.null_mask(), string_col.size(), @@ -736,7 +736,7 @@ struct string_to_decimal_impl { detail::string_to_decimal_kernel<<>>( data.data(), null_mask.data(), - string_col.chars().data(), + string_col.chars_begin(stream), string_col.offsets().data(), string_col.null_mask(), string_col.size(), diff --git a/src/main/cpp/src/format_float.cu b/src/main/cpp/src/format_float.cu index d9ecbe8206..3052d334aa 100644 --- a/src/main/cpp/src/format_float.cu +++ b/src/main/cpp/src/format_float.cu @@ -89,7 +89,7 @@ struct dispatch_format_float_fn { return cudf::make_strings_column(strings_count, std::move(offsets), - std::move(chars), + std::move(chars->release().data.release()[0]), floats.null_count(), cudf::detail::copy_bitmask(floats, stream, mr)); } diff --git a/src/main/cpp/src/map_utils.cu b/src/main/cpp/src/map_utils.cu index 002dadb0e3..9b420e201f 100644 --- a/src/main/cpp/src/map_utils.cu +++ b/src/main/cpp/src/map_utils.cu @@ -575,8 +575,11 @@ std::unique_ptr extract_keys_or_values( auto children = cudf::strings::detail::make_strings_children( substring_fn{unified_json_buff, extract_ranges}, num_extract, stream, mr); - return cudf::make_strings_column( - num_extract, std::move(children.first), std::move(children.second), 0, rmm::device_buffer{}); + return cudf::make_strings_column(num_extract, + std::move(children.first), + std::move(children.second->release().data.release()[0]), + 0, + rmm::device_buffer{}); } // Compute the offsets for the final lists of Struct.