strat: fix board namespacing for nintendo::nx

This commit is contained in:
Michael Scire 2020-12-29 12:30:43 -08:00
parent a26e8ac54f
commit 30e70e20d8
46 changed files with 57 additions and 57 deletions

View file

@ -18,7 +18,7 @@
#include <stratosphere/gpio/gpio_types.hpp> #include <stratosphere/gpio/gpio_types.hpp>
#include <stratosphere/gpio/driver/gpio_i_gpio_driver.hpp> #include <stratosphere/gpio/driver/gpio_i_gpio_driver.hpp>
namespace ams::gpio::driver::board::nintendo_nx { namespace ams::gpio::driver::board::nintendo::nx {
void Initialize(bool enable_interrupt_handlers); void Initialize(bool enable_interrupt_handlers);

View file

@ -26,7 +26,7 @@
namespace ams::gpio::driver::board { namespace ams::gpio::driver::board {
using namespace ams::gpio::driver::board::nintendo_nx; using namespace ams::gpio::driver::board::nintendo::nx;
} }

View file

@ -17,7 +17,7 @@
#include <vapours.hpp> #include <vapours.hpp>
#include <stratosphere/i2c/i2c_types.hpp> #include <stratosphere/i2c/i2c_types.hpp>
namespace ams::i2c::driver::board::nintendo_nx { namespace ams::i2c::driver::board::nintendo::nx {
void Initialize(); void Initialize();

View file

@ -25,7 +25,7 @@
namespace ams::i2c::driver::board { namespace ams::i2c::driver::board {
using namespace ams::i2c::driver::board::nintendo_nx; using namespace ams::i2c::driver::board::nintendo::nx;
} }

View file

@ -17,7 +17,7 @@
#include <vapours.hpp> #include <vapours.hpp>
#include <stratosphere/pwm/pwm_types.hpp> #include <stratosphere/pwm/pwm_types.hpp>
namespace ams::pwm::driver::board::nintendo_nx { namespace ams::pwm::driver::board::nintendo::nx {
void Initialize(); void Initialize();

View file

@ -24,7 +24,7 @@
namespace ams::pwm::driver::board { namespace ams::pwm::driver::board {
using namespace ams::pwm::driver::board::nintendo_nx; using namespace ams::pwm::driver::board::nintendo::nx;
} }

View file

@ -18,11 +18,11 @@
#include "impl/gpio_initial_config.hpp" #include "impl/gpio_initial_config.hpp"
#include "impl/gpio_tegra_pad.hpp" #include "impl/gpio_tegra_pad.hpp"
namespace ams::gpio::driver::board::nintendo_nx { namespace ams::gpio::driver::board::nintendo::nx {
namespace { namespace {
ams::gpio::driver::board::nintendo_nx::impl::DriverImpl *g_driver_impl = nullptr; ams::gpio::driver::board::nintendo::nx::impl::DriverImpl *g_driver_impl = nullptr;
} }
@ -38,7 +38,7 @@ namespace ams::gpio::driver::board::nintendo_nx {
AMS_ABORT_UNLESS(driver_storage != nullptr); AMS_ABORT_UNLESS(driver_storage != nullptr);
/* Construct the new driver. */ /* Construct the new driver. */
g_driver_impl = new (driver_storage) ams::gpio::driver::board::nintendo_nx::impl::DriverImpl(impl::GpioRegistersPhysicalAddress, impl::GpioRegistersSize); g_driver_impl = new (driver_storage) ams::gpio::driver::board::nintendo::nx::impl::DriverImpl(impl::GpioRegistersPhysicalAddress, impl::GpioRegistersSize);
/* Register the driver. */ /* Register the driver. */
gpio::driver::RegisterDriver(g_driver_impl); gpio::driver::RegisterDriver(g_driver_impl);

View file

@ -17,7 +17,7 @@
#include "gpio_driver_impl.hpp" #include "gpio_driver_impl.hpp"
#include "gpio_register_accessor.hpp" #include "gpio_register_accessor.hpp"
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
void InterruptEventHandler::Initialize(DriverImpl *drv, os::InterruptName intr, int ctlr) { void InterruptEventHandler::Initialize(DriverImpl *drv, os::InterruptName intr, int ctlr) {
/* Set fields. */ /* Set fields. */

View file

@ -20,7 +20,7 @@
#include "gpio_register_accessor.hpp" #include "gpio_register_accessor.hpp"
#include "gpio_suspend_handler.hpp" #include "gpio_suspend_handler.hpp"
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
class DriverImpl; class DriverImpl;
@ -43,7 +43,7 @@ namespace ams::gpio::driver::board::nintendo_nx::impl {
class DriverImpl : public ::ams::gpio::driver::IGpioDriver { class DriverImpl : public ::ams::gpio::driver::IGpioDriver {
NON_COPYABLE(DriverImpl); NON_COPYABLE(DriverImpl);
NON_MOVEABLE(DriverImpl); NON_MOVEABLE(DriverImpl);
AMS_DDSF_CASTABLE_TRAITS(ams::gpio::driver::board::nintendo_nx::impl::DriverImpl, ::ams::gpio::driver::IGpioDriver); AMS_DDSF_CASTABLE_TRAITS(ams::gpio::driver::board::nintendo::nx::impl::DriverImpl, ::ams::gpio::driver::IGpioDriver);
friend class InterruptEventHandler; friend class InterruptEventHandler;
private: private:
dd::PhysicalAddress gpio_physical_address; dd::PhysicalAddress gpio_physical_address;

View file

@ -18,7 +18,7 @@
#include "gpio_initial_config.hpp" #include "gpio_initial_config.hpp"
#include "gpio_wake_pin_config.hpp" #include "gpio_wake_pin_config.hpp"
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
namespace { namespace {

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
struct GpioInitialConfig { struct GpioInitialConfig {
DeviceCode device_code; DeviceCode device_code;

View file

@ -18,7 +18,7 @@
#include "gpio_tegra_pad.hpp" #include "gpio_tegra_pad.hpp"
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
constexpr inline dd::PhysicalAddress GpioRegistersPhysicalAddress = 0x6000D000; constexpr inline dd::PhysicalAddress GpioRegistersPhysicalAddress = 0x6000D000;
constexpr inline size_t GpioRegistersSize = 4_KB; constexpr inline size_t GpioRegistersSize = 4_KB;

View file

@ -16,7 +16,7 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "gpio_suspend_handler.hpp" #include "gpio_suspend_handler.hpp"
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
void SuspendHandler::Initialize(uintptr_t gpio_vaddr) { void SuspendHandler::Initialize(uintptr_t gpio_vaddr) {
/* Set our gpio virtual address. */ /* Set our gpio virtual address. */

View file

@ -18,7 +18,7 @@
#include "gpio_tegra_pad.hpp" #include "gpio_tegra_pad.hpp"
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
class SuspendHandler { class SuspendHandler {
NON_COPYABLE(SuspendHandler); NON_COPYABLE(SuspendHandler);

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
enum GpioPadPort { enum GpioPadPort {
GpioPadPort_A = 0, GpioPadPort_A = 0,
@ -347,7 +347,7 @@ namespace ams::gpio::driver::board::nintendo_nx::impl {
}; };
class TegraPad : public ::ams::gpio::driver::Pad { class TegraPad : public ::ams::gpio::driver::Pad {
AMS_DDSF_CASTABLE_TRAITS(ams::gpio::driver::board::nintendo_nx::impl::TegraPad, ::ams::gpio::driver::Pad); AMS_DDSF_CASTABLE_TRAITS(ams::gpio::driver::board::nintendo::nx::impl::TegraPad, ::ams::gpio::driver::Pad);
private: private:
using Base = ::ams::gpio::driver::Pad; using Base = ::ams::gpio::driver::Pad;
private: private:

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::gpio::driver::board::nintendo_nx::impl { namespace ams::gpio::driver::board::nintendo::nx::impl {
struct WakePinConfig { struct WakePinConfig {
wec::WakeEvent wake_event; wec::WakeEvent wake_event;

View file

@ -17,7 +17,7 @@
#include "impl/i2c_bus_manager.hpp" #include "impl/i2c_bus_manager.hpp"
#include "impl/i2c_device_property_manager.hpp" #include "impl/i2c_device_property_manager.hpp"
namespace ams::i2c::driver::board::nintendo_nx { namespace ams::i2c::driver::board::nintendo::nx {
namespace { namespace {

View file

@ -16,7 +16,7 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "i2c_bus_accessor.hpp" #include "i2c_bus_accessor.hpp"
namespace ams::i2c::driver::board::nintendo_nx::impl { namespace ams::i2c::driver::board::nintendo::nx::impl {
namespace { namespace {

View file

@ -17,12 +17,12 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "i2c_i2c_registers.hpp" #include "i2c_i2c_registers.hpp"
namespace ams::i2c::driver::board::nintendo_nx::impl { namespace ams::i2c::driver::board::nintendo::nx::impl {
class I2cBusAccessor : public ::ams::i2c::driver::II2cDriver { class I2cBusAccessor : public ::ams::i2c::driver::II2cDriver {
NON_COPYABLE(I2cBusAccessor); NON_COPYABLE(I2cBusAccessor);
NON_MOVEABLE(I2cBusAccessor); NON_MOVEABLE(I2cBusAccessor);
AMS_DDSF_CASTABLE_TRAITS(ams::i2c::driver::board::nintendo_nx::impl::I2cBusAccessor, ::ams::i2c::driver::II2cDriver); AMS_DDSF_CASTABLE_TRAITS(ams::i2c::driver::board::nintendo::nx::impl::I2cBusAccessor, ::ams::i2c::driver::II2cDriver);
private: private:
enum class State { enum class State {
NotInitialized = 0, NotInitialized = 0,

View file

@ -18,7 +18,7 @@
#include "i2c_bus_accessor.hpp" #include "i2c_bus_accessor.hpp"
#include "i2c_i_allocator.hpp" #include "i2c_i_allocator.hpp"
namespace ams::i2c::driver::board::nintendo_nx::impl { namespace ams::i2c::driver::board::nintendo::nx::impl {
class I2cBusAccessorManager : public IAllocator<I2cBusAccessor::BusAccessorList> { class I2cBusAccessorManager : public IAllocator<I2cBusAccessor::BusAccessorList> {
/* ... */ /* ... */

View file

@ -17,7 +17,7 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "i2c_i_allocator.hpp" #include "i2c_i_allocator.hpp"
namespace ams::i2c::driver::board::nintendo_nx::impl { namespace ams::i2c::driver::board::nintendo::nx::impl {
class I2cDevicePropertyManager : public IAllocator<I2cDeviceProperty::DevicePropertyList> { class I2cDevicePropertyManager : public IAllocator<I2cDeviceProperty::DevicePropertyList> {
/* ... */ /* ... */

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::i2c::driver::board::nintendo_nx::impl { namespace ams::i2c::driver::board::nintendo::nx::impl {
struct I2cRegisters { struct I2cRegisters {
volatile u32 cnfg; volatile u32 cnfg;

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::i2c::driver::board::nintendo_nx::impl { namespace ams::i2c::driver::board::nintendo::nx::impl {
template<typename ListType> template<typename ListType>
class IAllocator { class IAllocator {

View file

@ -18,7 +18,7 @@
#include "pinmux_board_driver_api.hpp" #include "pinmux_board_driver_api.hpp"
#include "pinmux_platform_pads.hpp" #include "pinmux_platform_pads.hpp"
namespace ams::pinmux::driver::board::nintendo_nx { namespace ams::pinmux::driver::board::nintendo::nx {
namespace { namespace {

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::pinmux::driver::board::nintendo_nx { namespace ams::pinmux::driver::board::nintendo::nx {
bool IsInitialized(); bool IsInitialized();

View file

@ -18,7 +18,7 @@
#include "pinmux_board_driver_api.hpp" #include "pinmux_board_driver_api.hpp"
#include "pinmux_platform_pads.hpp" #include "pinmux_platform_pads.hpp"
namespace ams::pinmux::driver::board::nintendo_nx { namespace ams::pinmux::driver::board::nintendo::nx {
namespace { namespace {

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::pinmux::driver::board::nintendo_nx { namespace ams::pinmux::driver::board::nintendo::nx {
struct PinmuxPadConfig { struct PinmuxPadConfig {
u32 index; u32 index;

View file

@ -20,7 +20,7 @@
#include "board/nintendo/nx/pinmux_board_driver_api.hpp" #include "board/nintendo/nx/pinmux_board_driver_api.hpp"
namespace ams::pinmux::driver::board { namespace ams::pinmux::driver::board {
using namespace ams::pinmux::driver::board::nintendo_nx; using namespace ams::pinmux::driver::board::nintendo::nx;
} }
#else #else

View file

@ -19,7 +19,7 @@
#include "powctl_battery_driver.hpp" #include "powctl_battery_driver.hpp"
#include "powctl_max17050_driver.hpp" #include "powctl_max17050_driver.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
namespace { namespace {

View file

@ -18,12 +18,12 @@
#include "../../../powctl_i_power_control_driver.hpp" #include "../../../powctl_i_power_control_driver.hpp"
#include "powctl_interrupt_event_handler.hpp" #include "powctl_interrupt_event_handler.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
class BatteryDevice : public powctl::impl::IDevice { class BatteryDevice : public powctl::impl::IDevice {
NON_COPYABLE(BatteryDevice); NON_COPYABLE(BatteryDevice);
NON_MOVEABLE(BatteryDevice); NON_MOVEABLE(BatteryDevice);
AMS_DDSF_CASTABLE_TRAITS(ams::powctl::impl::board::nintendo_nx::BatteryDevice, ::ams::powctl::impl::IDevice); AMS_DDSF_CASTABLE_TRAITS(ams::powctl::impl::board::nintendo::nx::BatteryDevice, ::ams::powctl::impl::IDevice);
private: private:
bool use_event_handler; bool use_event_handler;
std::optional<BatteryInterruptEventHandler> event_handler; std::optional<BatteryInterruptEventHandler> event_handler;
@ -43,7 +43,7 @@ namespace ams::powctl::impl::board::nintendo_nx {
class BatteryDriver : public IPowerControlDriver { class BatteryDriver : public IPowerControlDriver {
NON_COPYABLE(BatteryDriver); NON_COPYABLE(BatteryDriver);
NON_MOVEABLE(BatteryDriver); NON_MOVEABLE(BatteryDriver);
AMS_DDSF_CASTABLE_TRAITS(ams::powctl::impl::board::nintendo_nx::BatteryDriver, ::ams::powctl::impl::IPowerControlDriver); AMS_DDSF_CASTABLE_TRAITS(ams::powctl::impl::board::nintendo::nx::BatteryDriver, ::ams::powctl::impl::IPowerControlDriver);
public: public:
BatteryDriver(bool ev) : IPowerControlDriver(ev) { /* ... */ } BatteryDriver(bool ev) : IPowerControlDriver(ev) { /* ... */ }

View file

@ -19,7 +19,7 @@
#include "powctl_battery_driver.hpp" #include "powctl_battery_driver.hpp"
#include "powctl_charger_driver.hpp" #include "powctl_charger_driver.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
namespace { namespace {

View file

@ -18,7 +18,7 @@
#include "powctl_interrupt_event_handler.hpp" #include "powctl_interrupt_event_handler.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
void Initialize(bool use_event_handlers); void Initialize(bool use_event_handlers);
void Finalize(); void Finalize();

View file

@ -16,7 +16,7 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "powctl_bq24193_driver.hpp" #include "powctl_bq24193_driver.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
namespace bq24193 { namespace bq24193 {

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
namespace bq24193 { namespace bq24193 {

View file

@ -19,7 +19,7 @@
#include "powctl_charger_driver.hpp" #include "powctl_charger_driver.hpp"
#include "powctl_bq24193_driver.hpp" #include "powctl_bq24193_driver.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
namespace { namespace {

View file

@ -18,12 +18,12 @@
#include "../../../powctl_i_power_control_driver.hpp" #include "../../../powctl_i_power_control_driver.hpp"
#include "powctl_interrupt_event_handler.hpp" #include "powctl_interrupt_event_handler.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
class ChargerDevice : public powctl::impl::IDevice { class ChargerDevice : public powctl::impl::IDevice {
NON_COPYABLE(ChargerDevice); NON_COPYABLE(ChargerDevice);
NON_MOVEABLE(ChargerDevice); NON_MOVEABLE(ChargerDevice);
AMS_DDSF_CASTABLE_TRAITS(ams::powctl::impl::board::nintendo_nx::ChargerDevice, ::ams::powctl::impl::IDevice); AMS_DDSF_CASTABLE_TRAITS(ams::powctl::impl::board::nintendo::nx::ChargerDevice, ::ams::powctl::impl::IDevice);
private: private:
gpio::GpioPadSession gpio_pad_session; gpio::GpioPadSession gpio_pad_session;
bool watchdog_timer_enabled; bool watchdog_timer_enabled;
@ -54,7 +54,7 @@ namespace ams::powctl::impl::board::nintendo_nx {
class ChargerDriver : public IPowerControlDriver { class ChargerDriver : public IPowerControlDriver {
NON_COPYABLE(ChargerDriver); NON_COPYABLE(ChargerDriver);
NON_MOVEABLE(ChargerDriver); NON_MOVEABLE(ChargerDriver);
AMS_DDSF_CASTABLE_TRAITS(ams::powctl::impl::board::nintendo_nx::ChargerDriver, ::ams::powctl::impl::IPowerControlDriver); AMS_DDSF_CASTABLE_TRAITS(ams::powctl::impl::board::nintendo::nx::ChargerDriver, ::ams::powctl::impl::IPowerControlDriver);
public: public:
ChargerDriver(bool ev) : IPowerControlDriver(ev) { /* ... */ } ChargerDriver(bool ev) : IPowerControlDriver(ev) { /* ... */ }

View file

@ -16,7 +16,7 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "powctl_interrupt_event_handler.hpp" #include "powctl_interrupt_event_handler.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
void ChargerInterruptEventHandler::SignalEvent(IDevice *device) { void ChargerInterruptEventHandler::SignalEvent(IDevice *device) {
/* TODO */ /* TODO */

View file

@ -17,7 +17,7 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "../../../powctl_i_power_control_driver.hpp" #include "../../../powctl_i_power_control_driver.hpp"
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
template<typename Derived> template<typename Derived>
class InterruptEventHandler : public ddsf::IEventHandler { class InterruptEventHandler : public ddsf::IEventHandler {

View file

@ -20,7 +20,7 @@
#include <arm_neon.h> #include <arm_neon.h>
#endif #endif
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
namespace max17050 { namespace max17050 {

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::powctl::impl::board::nintendo_nx { namespace ams::powctl::impl::board::nintendo::nx {
namespace max17050 { namespace max17050 {

View file

@ -22,7 +22,7 @@
#include "board/nintendo/nx/powctl_board_impl.hpp" #include "board/nintendo/nx/powctl_board_impl.hpp"
namespace ams::powctl::impl::board { namespace ams::powctl::impl::board {
using namespace ams::powctl::impl::board::nintendo_nx; using namespace ams::powctl::impl::board::nintendo::nx;
} }
#else #else

View file

@ -17,7 +17,7 @@
#include "pwm_impl_pwm_driver_api.hpp" #include "pwm_impl_pwm_driver_api.hpp"
#include "pwm_pwm_driver_impl.hpp" #include "pwm_pwm_driver_impl.hpp"
namespace ams::pwm::driver::board::nintendo_nx::impl { namespace ams::pwm::driver::board::nintendo::nx::impl {
namespace { namespace {

View file

@ -16,7 +16,7 @@
#pragma once #pragma once
#include <stratosphere.hpp> #include <stratosphere.hpp>
namespace ams::pwm::driver::board::nintendo_nx::impl { namespace ams::pwm::driver::board::nintendo::nx::impl {
struct ChannelDefinition { struct ChannelDefinition {
DeviceCode device_code; DeviceCode device_code;

View file

@ -16,7 +16,7 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "pwm_pwm_driver_impl.hpp" #include "pwm_pwm_driver_impl.hpp"
namespace ams::pwm::driver::board::nintendo_nx::impl { namespace ams::pwm::driver::board::nintendo::nx::impl {
namespace { namespace {

View file

@ -17,12 +17,12 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "pwm_impl_pwm_driver_api.hpp" #include "pwm_impl_pwm_driver_api.hpp"
namespace ams::pwm::driver::board::nintendo_nx::impl { namespace ams::pwm::driver::board::nintendo::nx::impl {
class PwmDeviceImpl : public ::ams::pwm::driver::IPwmDevice { class PwmDeviceImpl : public ::ams::pwm::driver::IPwmDevice {
NON_COPYABLE(PwmDeviceImpl); NON_COPYABLE(PwmDeviceImpl);
NON_MOVEABLE(PwmDeviceImpl); NON_MOVEABLE(PwmDeviceImpl);
AMS_DDSF_CASTABLE_TRAITS(ams::pwm::driver::board::nintendo_nx::impl::PwmDeviceImpl, ::ams::pwm::driver::IPwmDevice); AMS_DDSF_CASTABLE_TRAITS(ams::pwm::driver::board::nintendo::nx::impl::PwmDeviceImpl, ::ams::pwm::driver::IPwmDevice);
private: private:
os::SdkMutex suspend_mutex; os::SdkMutex suspend_mutex;
u32 suspend_value; u32 suspend_value;
@ -39,7 +39,7 @@ namespace ams::pwm::driver::board::nintendo_nx::impl {
class PwmDriverImpl : public ::ams::pwm::driver::IPwmDriver { class PwmDriverImpl : public ::ams::pwm::driver::IPwmDriver {
NON_COPYABLE(PwmDriverImpl); NON_COPYABLE(PwmDriverImpl);
NON_MOVEABLE(PwmDriverImpl); NON_MOVEABLE(PwmDriverImpl);
AMS_DDSF_CASTABLE_TRAITS(ams::pwm::driver::board::nintendo_nx::impl::PwmDriverImpl, ::ams::pwm::driver::IPwmDriver); AMS_DDSF_CASTABLE_TRAITS(ams::pwm::driver::board::nintendo::nx::impl::PwmDriverImpl, ::ams::pwm::driver::IPwmDriver);
private: private:
dd::PhysicalAddress registers_phys_addr; dd::PhysicalAddress registers_phys_addr;
size_t registers_size; size_t registers_size;

View file

@ -16,7 +16,7 @@
#include <stratosphere.hpp> #include <stratosphere.hpp>
#include "impl/pwm_impl_pwm_driver_api.hpp" #include "impl/pwm_impl_pwm_driver_api.hpp"
namespace ams::pwm::driver::board::nintendo_nx { namespace ams::pwm::driver::board::nintendo::nx {
void Initialize() { void Initialize() {
R_ABORT_UNLESS(impl::InitializePwmDriver()); R_ABORT_UNLESS(impl::InitializePwmDriver());