From 53085a45e0b2cc995f4056de40116a66f7ae7c08 Mon Sep 17 00:00:00 2001 From: =?UTF-8?q?Viktor=20Sz=C3=A9pe?= Date: Sun, 7 Jan 2024 22:44:55 +0000 Subject: Fix typos in video_core --- src/video_core/buffer_cache/memory_tracker_base.h | 4 ++-- src/video_core/control/channel_state_cache.h | 4 ++-- src/video_core/control/channel_state_cache.inc | 2 +- src/video_core/engines/maxwell_3d.h | 10 +++++----- src/video_core/engines/sw_blitter/blitter.cpp | 8 ++++---- src/video_core/host1x/codecs/vp8.h | 2 +- src/video_core/host_shaders/astc_decoder.comp | 18 +++++++++--------- src/video_core/query_cache/query_cache.h | 2 +- src/video_core/query_cache/query_stream.h | 10 +++++----- .../renderer_vulkan/fixed_pipeline_state.cpp | 4 ++-- src/video_core/renderer_vulkan/fixed_pipeline_state.h | 2 +- src/video_core/renderer_vulkan/vk_blit_screen.h | 2 +- src/video_core/renderer_vulkan/vk_query_cache.cpp | 18 +++++++++--------- .../renderer_vulkan/vk_staging_buffer_pool.cpp | 4 ++-- src/video_core/renderer_vulkan/vk_texture_cache.cpp | 2 +- src/video_core/shader_environment.cpp | 6 +++--- src/video_core/vulkan_common/vulkan_device.h | 2 +- .../vulkan_common/vulkan_memory_allocator.cpp | 4 ++-- 18 files changed, 52 insertions(+), 52 deletions(-) diff --git a/src/video_core/buffer_cache/memory_tracker_base.h b/src/video_core/buffer_cache/memory_tracker_base.h index 6036b21c9..6c1c8287b 100644 --- a/src/video_core/buffer_cache/memory_tracker_base.h +++ b/src/video_core/buffer_cache/memory_tracker_base.h @@ -267,10 +267,10 @@ private: top_tier[page_index] = GetNewManager(base_cpu_addr); } - Manager* GetNewManager(VAddr base_cpu_addess) { + Manager* GetNewManager(VAddr base_cpu_address) { const auto on_return = [&] { auto* new_manager = free_managers.front(); - new_manager->SetCpuAddress(base_cpu_addess); + new_manager->SetCpuAddress(base_cpu_address); free_managers.pop_front(); return new_manager; }; diff --git a/src/video_core/control/channel_state_cache.h b/src/video_core/control/channel_state_cache.h index 5574e1fba..1dbfda299 100644 --- a/src/video_core/control/channel_state_cache.h +++ b/src/video_core/control/channel_state_cache.h @@ -85,12 +85,12 @@ protected: std::deque free_channel_ids; std::unordered_map channel_map; std::vector active_channel_ids; - struct AddresSpaceRef { + struct AddressSpaceRef { size_t ref_count; size_t storage_id; Tegra::MemoryManager* gpu_memory; }; - std::unordered_map address_spaces; + std::unordered_map address_spaces; mutable std::mutex config_mutex; virtual void OnGPUASRegister([[maybe_unused]] size_t map_id) {} diff --git a/src/video_core/control/channel_state_cache.inc b/src/video_core/control/channel_state_cache.inc index 460313893..31f792ddd 100644 --- a/src/video_core/control/channel_state_cache.inc +++ b/src/video_core/control/channel_state_cache.inc @@ -38,7 +38,7 @@ void ChannelSetupCaches

::CreateChannel(struct Tegra::Control::ChannelState& c as_it->second.ref_count++; return; } - AddresSpaceRef new_gpu_mem_ref{ + AddressSpaceRef new_gpu_mem_ref{ .ref_count = 1, .storage_id = address_spaces.size(), .gpu_memory = channel.memory_manager.get(), diff --git a/src/video_core/engines/maxwell_3d.h b/src/video_core/engines/maxwell_3d.h index 17faacc37..6b4f1c570 100644 --- a/src/video_core/engines/maxwell_3d.h +++ b/src/video_core/engines/maxwell_3d.h @@ -958,7 +958,7 @@ public: enum class ClearReport : u32 { ZPassPixelCount = 0x01, ZCullStats = 0x02, - StreamingPrimitvesNeededMinusSucceeded = 0x03, + StreamingPrimitivesNeededMinusSucceeded = 0x03, AlphaBetaClocks = 0x04, StreamingPrimitivesSucceeded = 0x10, StreamingPrimitivesNeeded = 0x11, @@ -2383,8 +2383,8 @@ public: }; enum class Release : u32 { - AfterAllPreceedingReads = 0, - AfterAllPreceedingWrites = 1, + AfterAllPrecedingReads = 0, + AfterAllPrecedingWrites = 1, }; enum class Acquire : u32 { @@ -2869,7 +2869,7 @@ public: u32 global_base_instance_index; ///< 0x1438 INSERT_PADDING_BYTES_NOINIT(0x14); RegisterWatermarks ps_warp_watermarks; ///< 0x1450 - RegisterWatermarks ps_regster_watermarks; ///< 0x1454 + RegisterWatermarks ps_register_watermarks; ///< 0x1454 INSERT_PADDING_BYTES_NOINIT(0xC); u32 store_zcull; ///< 0x1464 INSERT_PADDING_BYTES_NOINIT(0x18); @@ -3444,7 +3444,7 @@ ASSERT_REG_POSITION(invalidate_texture_header_cache_no_wfi, 0x1428); ASSERT_REG_POSITION(global_base_vertex_index, 0x1434); ASSERT_REG_POSITION(global_base_instance_index, 0x1438); ASSERT_REG_POSITION(ps_warp_watermarks, 0x1450); -ASSERT_REG_POSITION(ps_regster_watermarks, 0x1454); +ASSERT_REG_POSITION(ps_register_watermarks, 0x1454); ASSERT_REG_POSITION(store_zcull, 0x1464); ASSERT_REG_POSITION(iterated_blend_constants, 0x1480); ASSERT_REG_POSITION(load_zcull, 0x1500); diff --git a/src/video_core/engines/sw_blitter/blitter.cpp b/src/video_core/engines/sw_blitter/blitter.cpp index 3a599f466..67ce9134b 100644 --- a/src/video_core/engines/sw_blitter/blitter.cpp +++ b/src/video_core/engines/sw_blitter/blitter.cpp @@ -171,12 +171,12 @@ bool SoftwareBlitEngine::Blit(Fermi2D::Surface& src, Fermi2D::Surface& dst, const bool no_passthrough = src.format != dst.format || src_extent_x != dst_extent_x || src_extent_y != dst_extent_y; - const auto convertion_phase_same_format = [&]() { + const auto conversion_phase_same_format = [&]() { NearestNeighbor(impl->src_buffer, impl->dst_buffer, src_extent_x, src_extent_y, dst_extent_x, dst_extent_y, dst_bytes_per_pixel); }; - const auto convertion_phase_ir = [&]() { + const auto conversion_phase_ir = [&]() { auto* input_converter = impl->converter_factory.GetFormatConverter(src.format); impl->intermediate_src.resize_destructive((src_copy_size / src_bytes_per_pixel) * ir_components); @@ -211,9 +211,9 @@ bool SoftwareBlitEngine::Blit(Fermi2D::Surface& src, Fermi2D::Surface& dst, // Conversion Phase if (no_passthrough) { if (src.format != dst.format || config.filter == Fermi2D::Filter::Bilinear) { - convertion_phase_ir(); + conversion_phase_ir(); } else { - convertion_phase_same_format(); + conversion_phase_same_format(); } } else { impl->dst_buffer.swap(impl->src_buffer); diff --git a/src/video_core/host1x/codecs/vp8.h b/src/video_core/host1x/codecs/vp8.h index 7926b73f3..5945e4658 100644 --- a/src/video_core/host1x/codecs/vp8.h +++ b/src/video_core/host1x/codecs/vp8.h @@ -42,7 +42,7 @@ private: u8 raw; BitField<0, 2, u8> tile_format; BitField<2, 3, u8> gob_height; - BitField<5, 3, u8> reserverd_surface_format; + BitField<5, 3, u8> reserved_surface_format; }; u8 error_conceal_on; // 1: error conceal on; 0: off u32 first_part_size; // the size of first partition(frame header and mb header partition) diff --git a/src/video_core/host_shaders/astc_decoder.comp b/src/video_core/host_shaders/astc_decoder.comp index 5ff17cd0c..6e4535d45 100644 --- a/src/video_core/host_shaders/astc_decoder.comp +++ b/src/video_core/host_shaders/astc_decoder.comp @@ -803,7 +803,7 @@ void UnquantizeTexelWeights(uvec2 size, bool is_dual_plane) { } } -uint GetUnquantizedTexelWieght(uint offset_base, uint plane, bool is_dual_plane) { +uint GetUnquantizedTexelWeight(uint offset_base, uint plane, bool is_dual_plane) { const uint offset = is_dual_plane ? 2 * offset_base + plane : offset_base; return result_vector[offset]; } @@ -833,23 +833,23 @@ uvec4 GetUnquantizedWeightVector(uint t, uint s, uvec2 size, uint plane_index, b if (v0 < area) { const uint offset_base = v0; - p0.x = GetUnquantizedTexelWieght(offset_base, 0, is_dual_plane); - p1.x = GetUnquantizedTexelWieght(offset_base, 1, is_dual_plane); + p0.x = GetUnquantizedTexelWeight(offset_base, 0, is_dual_plane); + p1.x = GetUnquantizedTexelWeight(offset_base, 1, is_dual_plane); } if ((v0 + 1) < (area)) { const uint offset_base = v0 + 1; - p0.y = GetUnquantizedTexelWieght(offset_base, 0, is_dual_plane); - p1.y = GetUnquantizedTexelWieght(offset_base, 1, is_dual_plane); + p0.y = GetUnquantizedTexelWeight(offset_base, 0, is_dual_plane); + p1.y = GetUnquantizedTexelWeight(offset_base, 1, is_dual_plane); } if ((v0 + size.x) < (area)) { const uint offset_base = v0 + size.x; - p0.z = GetUnquantizedTexelWieght(offset_base, 0, is_dual_plane); - p1.z = GetUnquantizedTexelWieght(offset_base, 1, is_dual_plane); + p0.z = GetUnquantizedTexelWeight(offset_base, 0, is_dual_plane); + p1.z = GetUnquantizedTexelWeight(offset_base, 1, is_dual_plane); } if ((v0 + size.x + 1) < (area)) { const uint offset_base = v0 + size.x + 1; - p0.w = GetUnquantizedTexelWieght(offset_base, 0, is_dual_plane); - p1.w = GetUnquantizedTexelWieght(offset_base, 1, is_dual_plane); + p0.w = GetUnquantizedTexelWeight(offset_base, 0, is_dual_plane); + p1.w = GetUnquantizedTexelWeight(offset_base, 1, is_dual_plane); } const uint primary_weight = (uint(dot(p0, w)) + 8) >> 4; diff --git a/src/video_core/query_cache/query_cache.h b/src/video_core/query_cache/query_cache.h index efa9adf7a..94f0c4466 100644 --- a/src/video_core/query_cache/query_cache.h +++ b/src/video_core/query_cache/query_cache.h @@ -269,7 +269,7 @@ void QueryCacheBase::CounterReport(GPUVAddr addr, QueryType counter_type ASSERT(false); return; } - query_base->value += streamer->GetAmmendValue(); + query_base->value += streamer->GetAmendValue(); streamer->SetAccumulationValue(query_base->value); if (True(query_base->flags & QueryFlagBits::HasTimestamp)) { u64 timestamp = impl->gpu.GetTicks(); diff --git a/src/video_core/query_cache/query_stream.h b/src/video_core/query_cache/query_stream.h index 39da6ac07..d9040acd2 100644 --- a/src/video_core/query_cache/query_stream.h +++ b/src/video_core/query_cache/query_stream.h @@ -78,12 +78,12 @@ public: return dependence_mask; } - u64 GetAmmendValue() const { - return ammend_value; + u64 GetAmendValue() const { + return amend_value; } void SetAccumulationValue(u64 new_value) { - acumulation_value = new_value; + accumulation_value = new_value; } protected: @@ -95,8 +95,8 @@ protected: const size_t id; u64 dependence_mask; u64 dependent_mask; - u64 ammend_value{}; - u64 acumulation_value{}; + u64 amend_value{}; + u64 accumulation_value{}; }; template diff --git a/src/video_core/renderer_vulkan/fixed_pipeline_state.cpp b/src/video_core/renderer_vulkan/fixed_pipeline_state.cpp index e7df32d84..133ab0170 100644 --- a/src/video_core/renderer_vulkan/fixed_pipeline_state.cpp +++ b/src/video_core/renderer_vulkan/fixed_pipeline_state.cpp @@ -231,10 +231,10 @@ void FixedPipelineState::DynamicState::Refresh(const Maxwell& regs) { void FixedPipelineState::DynamicState::Refresh2(const Maxwell& regs, Maxwell::PrimitiveTopology topology_, - bool base_feautures_supported) { + bool base_features_supported) { logic_op.Assign(PackLogicOp(regs.logic_op.op)); - if (base_feautures_supported) { + if (base_features_supported) { return; } diff --git a/src/video_core/renderer_vulkan/fixed_pipeline_state.h b/src/video_core/renderer_vulkan/fixed_pipeline_state.h index 98ea20b42..dfe6d8032 100644 --- a/src/video_core/renderer_vulkan/fixed_pipeline_state.h +++ b/src/video_core/renderer_vulkan/fixed_pipeline_state.h @@ -165,7 +165,7 @@ struct FixedPipelineState { void Refresh(const Maxwell& regs); void Refresh2(const Maxwell& regs, Maxwell::PrimitiveTopology topology, - bool base_feautures_supported); + bool base_features_supported); void Refresh3(const Maxwell& regs); Maxwell::ComparisonOp DepthTestFunc() const noexcept { diff --git a/src/video_core/renderer_vulkan/vk_blit_screen.h b/src/video_core/renderer_vulkan/vk_blit_screen.h index 16b882b6d..78b32416d 100644 --- a/src/video_core/renderer_vulkan/vk_blit_screen.h +++ b/src/video_core/renderer_vulkan/vk_blit_screen.h @@ -130,7 +130,7 @@ private: vk::DescriptorPool descriptor_pool; vk::DescriptorSetLayout descriptor_set_layout; vk::PipelineLayout pipeline_layout; - vk::Pipeline nearest_neightbor_pipeline; + vk::Pipeline nearest_neighbor_pipeline; vk::Pipeline bilinear_pipeline; vk::Pipeline bicubic_pipeline; vk::Pipeline gaussian_pipeline; diff --git a/src/video_core/renderer_vulkan/vk_query_cache.cpp b/src/video_core/renderer_vulkan/vk_query_cache.cpp index 95954ade7..ad4caf688 100644 --- a/src/video_core/renderer_vulkan/vk_query_cache.cpp +++ b/src/video_core/renderer_vulkan/vk_query_cache.cpp @@ -120,8 +120,8 @@ public: scheduler{scheduler_}, memory_allocator{memory_allocator_} { current_bank = nullptr; current_query = nullptr; - ammend_value = 0; - acumulation_value = 0; + amend_value = 0; + accumulation_value = 0; queries_prefix_scan_pass = std::make_unique( device, scheduler, descriptor_pool, compute_pass_descriptor_queue); @@ -176,8 +176,8 @@ public: } AbandonCurrentQuery(); std::function func([this, counts = pending_flush_queries.size()] { - ammend_value = 0; - acumulation_value = 0; + amend_value = 0; + accumulation_value = 0; }); rasterizer->SyncOperation(std::move(func)); accumulation_since_last_sync = false; @@ -307,7 +307,7 @@ public: } ReplicateCurrentQueryIfNeeded(); - std::function func([this] { ammend_value = acumulation_value; }); + std::function func([this] { amend_value = accumulation_value; }); rasterizer->SyncOperation(std::move(func)); AbandonCurrentQuery(); num_slots_used = 0; @@ -512,7 +512,7 @@ private: pending_flush_queries.push_back(index); std::function func([this, index] { auto* query = GetQuery(index); - query->value += GetAmmendValue(); + query->value += GetAmendValue(); SetAccumulationValue(query->value); Free(index); }); @@ -1169,7 +1169,7 @@ struct QueryCacheRuntimeImpl { primitives_succeeded_streamer( static_cast(QueryType::StreamingPrimitivesSucceeded), runtime, tfb_streamer, cpu_memory_), - primitives_needed_minus_suceeded_streamer( + primitives_needed_minus_succeeded_streamer( static_cast(QueryType::StreamingPrimitivesNeededMinusSucceeded), runtime, 0u), hcr_setup{}, hcr_is_set{}, is_hcr_running{}, maxwell3d{} { @@ -1208,7 +1208,7 @@ struct QueryCacheRuntimeImpl { SamplesStreamer sample_streamer; TFBCounterStreamer tfb_streamer; PrimitivesSucceededStreamer primitives_succeeded_streamer; - VideoCommon::StubStreamer primitives_needed_minus_suceeded_streamer; + VideoCommon::StubStreamer primitives_needed_minus_succeeded_streamer; std::vector> little_cache; std::vector> buffers_to_upload_to; @@ -1433,7 +1433,7 @@ VideoCommon::StreamerInterface* QueryCacheRuntime::GetStreamerInterface(QueryTyp case QueryType::StreamingPrimitivesSucceeded: return &impl->primitives_succeeded_streamer; case QueryType::StreamingPrimitivesNeededMinusSucceeded: - return &impl->primitives_needed_minus_suceeded_streamer; + return &impl->primitives_needed_minus_succeeded_streamer; default: return nullptr; } diff --git a/src/video_core/renderer_vulkan/vk_staging_buffer_pool.cpp b/src/video_core/renderer_vulkan/vk_staging_buffer_pool.cpp index b278614e6..03a0b7280 100644 --- a/src/video_core/renderer_vulkan/vk_staging_buffer_pool.cpp +++ b/src/video_core/renderer_vulkan/vk_staging_buffer_pool.cpp @@ -236,14 +236,14 @@ void StagingBufferPool::ReleaseLevel(StagingBuffersCache& cache, size_t log2) { auto& entries = staging.entries; const size_t old_size = entries.size(); - const auto is_deleteable = [this](const StagingBuffer& entry) { + const auto is_deletable = [this](const StagingBuffer& entry) { return scheduler.IsFree(entry.tick); }; const size_t begin_offset = staging.delete_index; const size_t end_offset = std::min(begin_offset + deletions_per_tick, old_size); const auto begin = entries.begin() + begin_offset; const auto end = entries.begin() + end_offset; - entries.erase(std::remove_if(begin, end, is_deleteable), end); + entries.erase(std::remove_if(begin, end, is_deletable), end); const size_t new_size = entries.size(); staging.delete_index += deletions_per_tick; diff --git a/src/video_core/renderer_vulkan/vk_texture_cache.cpp b/src/video_core/renderer_vulkan/vk_texture_cache.cpp index 38b1619df..832b5e2b1 100644 --- a/src/video_core/renderer_vulkan/vk_texture_cache.cpp +++ b/src/video_core/renderer_vulkan/vk_texture_cache.cpp @@ -125,7 +125,7 @@ constexpr VkBorderColor ConvertBorderColor(const std::array& color) { MaxwellToVK::SurfaceFormat(device, FormatType::Optimal, false, info.format); VkImageCreateFlags flags{}; if (info.type == ImageType::e2D && info.resources.layers >= 6 && - info.size.width == info.size.height && !device.HasBrokenCubeImageCompability()) { + info.size.width == info.size.height && !device.HasBrokenCubeImageCompatibility()) { flags |= VK_IMAGE_CREATE_CUBE_COMPATIBLE_BIT; } if (info.type == ImageType::e3D) { diff --git a/src/video_core/shader_environment.cpp b/src/video_core/shader_environment.cpp index 492440ac4..250fde96c 100644 --- a/src/video_core/shader_environment.cpp +++ b/src/video_core/shader_environment.cpp @@ -322,7 +322,7 @@ GraphicsEnvironment::GraphicsEnvironment(Tegra::Engines::Maxwell3D& maxwell3d_, ASSERT(local_size <= std::numeric_limits::max()); local_memory_size = static_cast(local_size) + sph.common3.shader_local_memory_crs_size; texture_bound = maxwell3d->regs.bindless_texture_const_buffer_slot; - is_propietary_driver = texture_bound == 2; + is_proprietary_driver = texture_bound == 2; has_hle_engine_state = maxwell3d->engine_state == Tegra::Engines::Maxwell3D::EngineHint::OnHLEMacro; } @@ -404,7 +404,7 @@ ComputeEnvironment::ComputeEnvironment(Tegra::Engines::KeplerCompute& kepler_com stage = Shader::Stage::Compute; local_memory_size = qmd.local_pos_alloc + qmd.local_crs_alloc; texture_bound = kepler_compute->regs.tex_cb_index; - is_propietary_driver = texture_bound == 2; + is_proprietary_driver = texture_bound == 2; shared_memory_size = qmd.shared_alloc; workgroup_size = {qmd.block_dim_x, qmd.block_dim_y, qmd.block_dim_z}; } @@ -509,7 +509,7 @@ void FileEnvironment::Deserialize(std::ifstream& file) { file.read(reinterpret_cast(&gp_passthrough_mask), sizeof(gp_passthrough_mask)); } } - is_propietary_driver = texture_bound == 2; + is_proprietary_driver = texture_bound == 2; } void FileEnvironment::Dump(u64 pipeline_hash, u64 shader_hash) { diff --git a/src/video_core/vulkan_common/vulkan_device.h b/src/video_core/vulkan_common/vulkan_device.h index 701817086..a2ec26697 100644 --- a/src/video_core/vulkan_common/vulkan_device.h +++ b/src/video_core/vulkan_common/vulkan_device.h @@ -596,7 +596,7 @@ public: } /// Returns true when the device does not properly support cube compatibility. - bool HasBrokenCubeImageCompability() const { + bool HasBrokenCubeImageCompatibility() const { return has_broken_cube_compatibility; } diff --git a/src/video_core/vulkan_common/vulkan_memory_allocator.cpp b/src/video_core/vulkan_common/vulkan_memory_allocator.cpp index 8dd1667f3..8f4a57e3c 100644 --- a/src/video_core/vulkan_common/vulkan_memory_allocator.cpp +++ b/src/video_core/vulkan_common/vulkan_memory_allocator.cpp @@ -57,7 +57,7 @@ struct Range { return VK_MEMORY_PROPERTY_HOST_VISIBLE_BIT | VK_MEMORY_PROPERTY_HOST_COHERENT_BIT; } -[[nodiscard]] VkMemoryPropertyFlags MemoryUsagePreferedVmaFlags(MemoryUsage usage) { +[[nodiscard]] VkMemoryPropertyFlags MemoryUsagePreferredVmaFlags(MemoryUsage usage) { return usage != MemoryUsage::DeviceLocal ? VK_MEMORY_PROPERTY_HOST_COHERENT_BIT : VkMemoryPropertyFlagBits{}; } @@ -256,7 +256,7 @@ vk::Buffer MemoryAllocator::CreateBuffer(const VkBufferCreateInfo& ci, MemoryUsa .flags = VMA_ALLOCATION_CREATE_WITHIN_BUDGET_BIT | MemoryUsageVmaFlags(usage), .usage = MemoryUsageVma(usage), .requiredFlags = 0, - .preferredFlags = MemoryUsagePreferedVmaFlags(usage), + .preferredFlags = MemoryUsagePreferredVmaFlags(usage), .memoryTypeBits = usage == MemoryUsage::Stream ? 0u : valid_memory_types, .pool = VK_NULL_HANDLE, .pUserData = nullptr, -- cgit v1.2.3