主页 / coding / 问题

问题[arm](coding)

Martin Hope
Furlings
Asked: 2024-12-15 19:49:47 +0800 CST
  • 6

该gdb命令set substitute-path未按预期工作。我有一个.elfarm 文件，我想用源路径替换调试：

C:\Users\user\Desktop\project\src/main.c:

到

./src/main.c:

我尝试了以下命令，但没有成功：

>>> set substitute-path C:\\Users\\user\\Desktop\\project\\ \.//
>>> show substitute-path
List of all source path substitution rules:
  `C:\Users\user\Desktop\project\' -> `./'.

>>> list main
40      C:\Users\user\Desktop\project\src/main.c: No such file or directory.

我也尝试了很多不同的替代路径，但没有成功：

set substitute-path C:\Users\user\Desktop\project\ ./
...
set substitute-path C:\\Users\\user\\Desktop\\project\\ ./
...
...

我想知道我是否正确使用了该set substitute-path命令。

arm
Martin Hope
Zvi Vered
Asked: 2024-09-17 05:44:18 +0800 CST
  • 5

我有以下输入：

[1i+2j], [3i+4j], [5i+6j],...

输出应为：

[1i+2j], [0i+0j], [3i+4j], [0i+0j], [5i+6j], [0i+0j],...

我写了以下代码：

void Extract (ComplexFloat *pIn, ComplexFloat*pOut, uint32_t N)
{
    ComplexFloat* pSrc = pIn;
    ComplexFloat *pDst = (ComplexFloat*)pOut;
    float32x2_t Zero;
    float32x4_t In, Out;
    float32x2_t HighIn, LowIn;

    Zero = vdup_n_f32 (0);

    //Loop on all input elements 
    for (int n = 0; n < N >> 1; n++)
    {
        In = vld1q_f32((float*)pSrc);
        HighIn = vget_high_f32(In);
        LowIn = vget_low_f32(In);
        Out = vcombine_f32(LowIn, Zero);
        vst1q_f32((float*)pDst, Out);
        pDst += 2;
        Out = vcombine_f32(HighIn, Zero);
        vst1q_f32((float*)pDst, Out);
        pDst += 2;
        pSrc += 2;
    }

}

您能推荐一个性能更好的代码吗？

谢谢你，Zvika

arm
Martin Hope
user2953113
Asked: 2024-07-06 12:41:43 +0800 CST
  • 5

我是 STM32 微控制器的新手。我想知道如何在启用 RCC 外设时钟后正确实现 2 个时钟周期的延迟。

https://www.st.com/resource/en/reference_manual/rm0454-stm32g0x0-advanced-armbased-32bit-mcus-stmicroelectronics.pdf的第 5.2.16 节（第 134 页）

使能位具有同步机制，可为外设创建无故障时钟。设置使能位后，时钟激活前会有 2 个时钟周期的延迟，软件必须考虑到这一点。

我偶然发现了下面的解释，它看起来是正确的。

https://github.com/lab11/stm32l0-base/blob/master/sdk/STM32Cube_FW_LO_V1.5.0/Drivers/STM32L0xx_HAL_Driver/Src/stm32l0xx_hal_rcc.c >

RCC 限制##### 评论部分。

此延迟取决于外设映射。如果外设映射到 AHB 上：在硬件寄存器上设置时钟使能位后，延迟为 2 个 AHB 时钟周期。如果外设映射到 APB 上：在硬件寄存器上设置时钟使能位后，延迟为 2 个 APB 时钟周期。

我看了几个例子。第一个例子中，读回了 RCC 外设时钟使能寄存器。

RCC->AHB1ENR |= (1 << RCC_AHB1ENR_GPIOAEN_Pos);
  
// do two dummy reads after enabling the peripheral clock, as per the errata
volatile uint32_t dummy;
dummy = RCC->AHB1ENR;
dummy = RCC->AHB1ENR;

第二个例子中，读回外设寄存器。

void clock_wait_bus_cycles(enum bus_type bus, uint32_t cycles)
{
    volatile uint32_t unused __attribute__((unused));
    if (bus == BUS_AHB) {
        while (cycles--)
            unused = STM32_DMA1_REGS->isr;
    } else { /* APB */
        while (cycles--)
            unused = STM32_USART_BRR(STM32_USART1_BASE);
    }
}

哪一个才是正确的方法？

arm
Martin Hope
Yiyang Yan
Asked: 2024-01-10 05:11:09 +0800 CST
  • 5

最近我开始学习 ThreadX RTOS，我注意到在链接器脚本中，并crt0.S为 Cortex-M4 提供了 gcc 工具链，.stack并且.heap段的大小分别分配为 1024 字节和 128 字节。

在编写了一个在字节池上静态创建 2 个线程的简单程序后，我运行了objdump -t program.elf. 原来，为字节池、线程控制块和其他ThreadX变量、指针分配的内存都在该.bss节中。

.stack我想知道创建和分区的目的是什么.heap。它们是否存在以防调用动态内存分配函数（例如mallocC 标准库（newlib）中的动态内存分配函数）？

arm
Martin Hope
Martin Chekurov
Asked: 2023-08-27 22:13:42 +0800 CST
  • 5

我正在学习 ARM 上的裸机编程如何工作，但我很难理解如何使用链接器脚本中定义的地址。

这是我的链接器脚本：

ENTRY(ResetHandler)

MEMORY
{
    ROM (rx) : ORIGIN = 0x08000000, LENGTH = 512K
    RAM (rwx) : ORIGIN = 0x20000000, LENGTH = 128K
}

SECTIONS
{
    .text :
    {
        KEEP(*(.isr_vector))
        *(.text)
        *(.text.*)
        *(.rodata)
        *(.rodata.*)
        . = ALIGN(4);
        _etext = .;
    }>ROM AT>ROM

    .data :
    {
        _sdata = .;
        *(.data)
        *(.data.*)
        . = ALIGN(4);
        _edata = .;
    }>RAM AT>ROM

    .bss (NOLOAD) :
    {
        _sbss = .;
        *(.bss)
        *(.bss.*)
        *(COMMON)
        . = ALIGN(4);
        _ebss = .;
    }>RAM AT>ROM
}

所有节的地址都在链接器文件中描述。我不明白的是，我的最终编译结果是一个原始二进制文件，仅包含代码和数据，没有地址。加载此二进制文件时，当我在加载过程中除了二进制文件之外没有指定任何内容时，如何将这些节定位到链接器文件中定义的正确地址？链接描述文件中有关 LMA 和 VMA 的所有信息都会丢失。这一切都是由引导加载程序执行的吗？

arm