• EDSCR err bit set after a write to EDITR

    kka
    kka

    Hi,

    I have a very similar question to the resolved entry "reason for ARMv8 EDSCR err bit set".

    So I try to follow that to give the state information.

    Cortex-57

    JTAG TCK = 3,788MHz.

    ARM_STATE_AARCH64 is set

    Before Halt state:

    EDPRSR = 0x1

    EDSCR…

    • 4 months ago
    • Processors
    • Cortex-A / A-Profile forum
  • Why does Arm still support short descriptors?

    DarkDante
    DarkDante

    What I'm asking is ARM Architecture Reference Manual for ARMv8-A  says in AArch32 there are two translation table formats:

    • Short descriptors: 32 bit
    • Long descriptors: 64 bit

    On page G4-4726 (Issue B.b), there are various points listed that each…

    • 4 months ago
    • Processors
    • Cortex-A / A-Profile forum
  • What can cause getting Cortex-A55 DSU P-Channel PACCEPT/PDENY signals fail?

    Emmy0
    Emmy0

    Hi experts,

    I do an experiment about cpu power with a board which has 4 cores of Cortex-A55.

    I try to power on/power off core1~3 parallelly.

    Sometimes Both PACCEPT and PDENY are zero after changes the power state.

    If I only power on/power off one core,…

    • 5 months ago
    • Processors
    • Cortex-A / A-Profile forum
  • [ArmV8] [Cortex-A53] [PMU] PM_CCNTR to measure cpuload

    Amr Fawzy
    Amr Fawzy

    Dear Experts

    I am working on a target that contains quad A53 cores operating at 1GHz. The operating system idle loop contains WFI inline assembly instruction. I know that the Core Clock halts during the WFI instruction which can be seen on the PM_CCNTR…

    • 5 months ago
    • Processors
    • Cortex-A / A-Profile forum
  • The "usage model" of ARMv8 SVE contiguous "non-fault" load instructions ?

    alexn
    alexn

    Hello,

    What exactly is the "usage model" of ARMv8 SVE contiguous "non-fault" load instructions ?

    I understand the usage model of "first-fault" SVE instrcutions (which is described in many white papers) but the "usage model" of ARMv8…

    • 5 months ago
    • Processors
    • Cortex-A / A-Profile forum
  • Enabling Cloud-Native Experience Across a Diverse and Secure Edge Ecosystem

    P. Robin
    P. Robin

    The launch of Arm Neoverse was a foundation for cloud to edge infrastructure. Arm has significantly increased its investment in the Cloud Native ecosystem. After joining the Cloud Native Foundation in February 2019, this week we are moving a step further…

    • 7 months ago
    • Software Tools
    • Tools, Software and IDEs blog
  • System Frequency for CortexA35

    M.Eladouly
    M.Eladouly

    Hello,

    For a CortexA35, when reading the system counter clock frequency CNTFRQ_EL0, I found out that the frequency is 8 MHz.

    Is this normal? For a target running in GHz?

    The target is i.MX8QXP (Quad-Core CortexA35).

    • Answered
    • 7 months ago
    • Processors
    • Cortex-A / A-Profile forum
  • Why ARM does not support 64bit for faulting address of IPA?

    YOO JEUNGWOO
    YOO JEUNGWOO

    I'm trying to understand how ARM architecture(ARMv8) support for faulting address in the virtualization environment. For the hypervisor, every device access from the guest must be trapped to emulate a device.

    The memory access from the guest will…

    • Answered
    • 8 months ago
    • Processors
    • Cortex-M / M-Profile forum
  • What are the necessary preconditions to load a guest into EL1 from EL2?

    Branden Sherrell
    Branden Sherrell

    I have successfully moved from EL3 to EL2. After doing some initialization I am trying to move from EL2 into EL1 with a very simple guest image. My process looks like:

    • Map EL1 memory into EL2
    • Copy EL1 image to RAM
    • Initialize sctlr_el1 = 0x30d00800
      …
      • Answered
      • 8 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • Setting PC for and waking up secondary cores from the primary core

      Branden Sherrell
      Branden Sherrell

      Given a multiprocessor system, how are the PC values of secondary cores set from the primary core? I've read lots of threads stating it can be done but without any details. I could not find anything in the ARMv8 reference manual.

      One might contrive…

      • Answered
      • 9 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • Developments in the Arm A-Profile Architecture: Armv8.6-A

      Nigel Stephens
      Nigel Stephens

      The Arm Architecture is continually evolving to meet the needs of our ecosystem partners. This blog gives a high-level overview of some of the changes being introduced in Armv8.6-A.

      The enhancements to the architecture provide more efficient processing…

      • 8 months ago
      • Processors
      • Processors blog
    • Difference between ARMv8 Data Abort exception subtypes "Not in translation table" and "Translation table fault at level"?

      Branden Sherrell
      Branden Sherrell
      I've gotten virtual memory working on ARMv8 after crafting the page tables. Oddly, _most_ of my translations are working (identity mapped) save for Flash which sits at physical address zero. I use a single function that edits the page tables, so the fact…
      • Answered
      • 9 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • ARMv8 memory ordering

      roffelsen
      roffelsen

      In the ARM Architecture Reference Manual issue D.a (ARM DDI 0487D.a) section K11.3.1 "Acquiring a lock" has the following example code:

      AArch32 
      Px
              PLDW[R1]                     ; preload into cache in unique state
      Loop
              LDAEX R5, [R1]               ; read…
      • Answered
      • 9 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • Getting Execution Time of progams on armv8_64-bit processors

      abhi.verma
      abhi.verma

      I have written a library for ARMv8-A 64 bit processors (OS- linaro debian). Now I want to time them. I am utilising gcc compiler and on Intel processors I was timing the execution utilising std::chrono high resolution clock. The issue with arm is, it…

      • Answered
      • 9 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • Obtain CPU Temperature in Kernel

      zzT
      zzT

       Dear All,

      I am using a raspberry pi B+ that uses a Broadcom BCM2837 SoC with an ARMV8  processor. I want to get the cpu temperature in a Linux kernel file. Like in x86, I can use rdmsr_on_cpu function to load the temperature from MSR_IA32_THERM_STATUS register…

      • 9 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • BFloat16 processing for Neural Networks on Armv8-A

      Nigel Stephens
      Nigel Stephens

      Neural Networks are a key component of Machine Learning (ML) applications. Project Trillium, Arm’s heterogeneous ML platform, provides a range of technologies in this field, including instructions that accelerate such applications running on CPUs based…

      • 9 months ago
      • Processors
      • Machine Learning IP blog
    • What is arrangement specifier(.16b,.8b) in ARM assembly language instructions?

      surajrgupta
      surajrgupta

      I want to what exactly is arrangement specifier in arm assembly instructions.

      I have gone through ARM TRMs and i think if it is size of Neon register that will be used for computation

      for e.g. TBL Vd.Ta, {Vn.16B,Vn+1.16B }, Vm.Ta

      they mentioned Ta to…

      • 10 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • ARMv8 PMU access

      Jorge
      Jorge

      Hey guys,

      I'm running a sw in a multicore ARMv8 system and I'd like to know a bit more about the PMU component. There is a PMU per CPU, right? 

      Is it possible from one CPU to access the other CPU's PMU using the memory mapped interface?

      …
      • 10 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • determine a page size on armv8

      MarekBykowski
      MarekBykowski

      Hi,

      I have a need at determining a page size, particularly for a Non-secure EL1, stage 1. I know of 

      __asm__ volatile ("at s1e1r, %0" : : "r" (buf));    
      __asm__ volatile ("mrs %0, PAR_EL1\n" : "=r" (par_el1));

      …
      • Answered
      • 10 months ago
      • Processors
      • Cortex-A / A-Profile forum
    • What is the difference between ARM cortex-A and cores in snapdragon from Qualcomm?

      Nitin Bhaskar
      Nitin Bhaskar

      Hi All,

      What is the difference between ARM cortex-A and cores in snapdragon from Qualcomm? I know that they say it is compatible with ARMv7/8 ISA.

      Regards

      Nitin

      • Answered
      • over 4 years ago
      • Processors
      • Cortex-A / A-Profile forum
    • ARMv8-A:TrustZone and MMU

      42Bastian
      42Bastian

      I wonder how VA->PA translation is handled from non-secure world with Aarch64.

      I see the HYP mode uses IPA so that the second stage translation may restrict the VM to certain memory.

      But what about limiting access to secure memory? Is it only possible…

      • Answered
      • over 4 years ago
      • Processors
      • Cortex-A / A-Profile forum
    • I'm not seeing any flush-to-zero (FTZ) effects with NEON intrinsics on an ARM A9, any advice?

      David L
      David L

      Hi everyone,

      As the title states - I've had issues reproducing flush-to-zero (FTZ) using the NEON intrinsics provided in the 'arm_neon.h' header. For test purposes I'm using an iPhone 6 with an ARMv8-A dual-core ('Twister') CPU.…

      • Answered
      • over 4 years ago
      • Processors
      • Cortex-A / A-Profile forum
    • How to configure Cortex-A57 PMU

      Michael
      Michael

      I asked this question in a different community space but it seemed like this is a more appropriate home.

      I'm trying to configure the performance counters for the Cortex-A57 and I'm very confused. The technical reference manual alludes to accesses being…

      • Answered
      • over 4 years ago
      • Processors
      • Cortex-A / A-Profile forum
    • How to use generic timer/counter

      Michael
      Michael

      The technical reference manual states that the Cortex-A57 generic timer events are not affected by CPU clock frequency change. My challenge is that I can't use any built in linux libraries to create a delay because whenever I try it clears performance…

      • Answered
      • over 4 years ago
      • Processors
      • Cortex-A / A-Profile forum
    • How to do the ARM state change between 64-bit and 32-bit?

      Prasad
      Prasad

      Hi,

      The latest 64-bit architecture can on both AArch64 and AArch32 state.

      Can someone tell me how to utilize this feature so that I can seamlessly integrate algorithms (which are optimized with 32-bit and 64-bit instructions) with applications which are…

      • Answered
      • over 4 years ago
      • Processors
      • Cortex-A / A-Profile forum
    <>