andrew (Andrew Turner)
User

Projects

User Details

User Since
May 10 2014, 2:21 PM (223 w, 3 d)

Recent Activity

Thu, Aug 16

andrew committed rS337903: Remove the L1 and L2 xscale page defines and rename the generic macros to.
Remove the L1 and L2 xscale page defines and rename the generic macros to
Thu, Aug 16, 10:01 AM

Wed, Aug 15

andrew committed rS337853: Remove pmap_kenter_section from the arm pmap. It's unused..
Remove pmap_kenter_section from the arm pmap. It's unused.
Wed, Aug 15, 2:57 PM
andrew committed rS337851: Remove ARM_HAVE_SUPERSECTIONS. It was only supported on some XScale CPUs..
Remove ARM_HAVE_SUPERSECTIONS. It was only supported on some XScale CPUs.
Wed, Aug 15, 2:53 PM
andrew committed rS337850: Make code and data only used within the arm pmap code as static..
Make code and data only used within the arm pmap code as static.
Wed, Aug 15, 2:45 PM
andrew committed rS337848: Remove arm pmap variables that are only ever set and never read..
Remove arm pmap variables that are only ever set and never read.
Wed, Aug 15, 2:29 PM
andrew committed rS337847: Remove ARM_MMU_GENERIC, it's the only ARMV4/v5 MMU we support..
Remove ARM_MMU_GENERIC, it's the only ARMV4/v5 MMU we support.
Wed, Aug 15, 2:19 PM
andrew committed rS337846: Remove the ARMv5 pmap function pointers. These were to support XScale so.
Remove the ARMv5 pmap function pointers. These were to support XScale so
Wed, Aug 15, 1:52 PM
andrew committed rS337845: Remove checks for now unsupported CPU_* values in arm headers..
Remove checks for now unsupported CPU_* values in arm headers.
Wed, Aug 15, 1:49 PM
andrew committed rS337843: Start to remove XScale support from the ARMv4/v5 pmap. Support for XScale.
Start to remove XScale support from the ARMv4/v5 pmap. Support for XScale
Wed, Aug 15, 1:40 PM
andrew committed rS337842: Set the Execute Never flags in EFI device memory as required by the ARMv8.
Set the Execute Never flags in EFI device memory as required by the ARMv8
Wed, Aug 15, 1:19 PM
andrew committed rS337841: Remove PHYSADDR from kernel configurations that don't need it. The only.
Remove PHYSADDR from kernel configurations that don't need it. The only
Wed, Aug 15, 1:13 PM
andrew committed rS337839: Remove the VIRT armv7 kernel config. It is supported by GENERIC..
Remove the VIRT armv7 kernel config. It is supported by GENERIC.
Wed, Aug 15, 1:03 PM

Tue, Aug 14

andrew committed rS337762: Remove cpu_pfr from arm. It's unused..
Remove cpu_pfr from arm. It's unused.
Tue, Aug 14, 4:01 PM
andrew committed rS337761: Remove an old comment now the code it references has been removed..
Remove an old comment now the code it references has been removed.
Tue, Aug 14, 3:48 PM
andrew committed rS337760: Fix the spelling of armv4_idcache_inv_all in an END macro..
Fix the spelling of armv4_idcache_inv_all in an END macro.
Tue, Aug 14, 3:42 PM
andrew committed rS337739: Support reading from the arm64 ID registers from userspace..
Support reading from the arm64 ID registers from userspace.
Tue, Aug 14, 11:01 AM
andrew closed D16533: Support reading from the arm64 ID registers from userspace.
Tue, Aug 14, 11:01 AM

Tue, Aug 7

andrew added inline comments to D16614: [evdev]: Minor KPI changes.
Tue, Aug 7, 11:43 AM

Mon, Aug 6

andrew committed rS337379: Default to armv5te in LINT on arm. This should fix building LINT there..
Default to armv5te in LINT on arm. This should fix building LINT there.
Mon, Aug 6, 2:41 PM

Tue, Jul 31

andrew created D16533: Support reading from the arm64 ID registers from userspace.
Tue, Jul 31, 6:29 PM
andrew committed rS336971: Use int for the pcpu_ssbd argument. This is included from userland and may.
Use int for the pcpu_ssbd argument. This is included from userland and may
Tue, Jul 31, 3:08 PM
andrew committed rS336967: Implement the SSBD (CVE-2018-3639) workaround on arm64.
Implement the SSBD (CVE-2018-3639) workaround on arm64
Tue, Jul 31, 12:54 PM
andrew closed D15819: Implement the SSBD (CVE-2018-3639) workaround on arm64.
Tue, Jul 31, 12:53 PM

Mon, Jul 30

andrew committed rS336915: Enable VIMAGE on arm64 again. A workaround for modules with static VNET.
Enable VIMAGE on arm64 again. A workaround for modules with static VNET
Mon, Jul 30, 3:58 PM
andrew committed rS336909: As with DPCPU_DEFINE_STATIC make VNET_DEFINE_STATIC non-static on arm64 in.
As with DPCPU_DEFINE_STATIC make VNET_DEFINE_STATIC non-static on arm64 in
Mon, Jul 30, 3:05 PM
andrew committed rS336906: Ensure the DPCPU and VNET module spaces are aligned to hold a pointer..
Ensure the DPCPU and VNET module spaces are aligned to hold a pointer.
Mon, Jul 30, 2:25 PM
andrew committed rS336902: As with DPCPU_DEFINE make it a compile error to use static with VNET_DEFINE..
As with DPCPU_DEFINE make it a compile error to use static with VNET_DEFINE.
Mon, Jul 30, 12:45 PM
andrew committed rS336894: Remove teh non-INTRNG code from the ARM GIC interrupt controller driver..
Remove teh non-INTRNG code from the ARM GIC interrupt controller driver.
Mon, Jul 30, 10:55 AM
andrew committed rS336892: Require ARMv5 for arm. All current kernels are for ARMv5 or later, and it.
Require ARMv5 for arm. All current kernels are for ARMv5 or later, and it
Mon, Jul 30, 9:50 AM

Sat, Jul 28

andrew committed rS336834: Use the cp15 functions to read cp15 registers rather than using assembly.
Use the cp15 functions to read cp15 registers rather than using assembly
Sat, Jul 28, 5:21 PM
andrew committed rS336833: Remove an unneeded cpu_ident() prototype..
Remove an unneeded cpu_ident() prototype.
Sat, Jul 28, 4:57 PM
andrew committed rS336831: Remove some write only global values from the arm cpufunc code..
Remove some write only global values from the arm cpufunc code.
Sat, Jul 28, 12:53 PM
andrew committed rS336830: Remove an unused function from the arm ELF trampoline. It tries to find.
Remove an unused function from the arm ELF trampoline. It tries to find
Sat, Jul 28, 12:52 PM
andrew committed rS336829: Only build the cache handling code we need when building the arm ELF.
Only build the cache handling code we need when building the arm ELF
Sat, Jul 28, 12:50 PM
andrew committed rS336828: Make the arm cpu setup functions static. Any other place that needs these.
Make the arm cpu setup functions static. Any other place that needs these
Sat, Jul 28, 12:20 PM
andrew committed rS336827: Remove an unneeded check for CPU_XSCALE_81342.
Remove an unneeded check for CPU_XSCALE_81342
Sat, Jul 28, 12:17 PM
andrew committed rS336826: Remove old CPU_ values from the arm cpufunc code. These have been removed..
Remove old CPU_ values from the arm cpufunc code. These have been removed.
Sat, Jul 28, 12:00 PM
andrew committed rS336825: Remove the old CPU_ values from the arm kernel trampoline. These options.
Remove the old CPU_ values from the arm kernel trampoline. These options
Sat, Jul 28, 11:59 AM
andrew committed rS336813: Remove now the cow unused CPU_ARM9 and CPU_FA526 options. These are for.
Remove now the cow unused CPU_ARM9 and CPU_FA526 options. These are for
Sat, Jul 28, 11:00 AM
andrew committed rS336807: The RT1310 is an ARM926EJ-S, fix the config to mark it as such..
The RT1310 is an ARM926EJ-S, fix the config to mark it as such.
Sat, Jul 28, 10:49 AM
andrew committed rS336804: Remove IPI_IRQ_START and IPI_IRQ_END from the arm kernel config files..
Remove IPI_IRQ_START and IPI_IRQ_END from the arm kernel config files.
Sat, Jul 28, 6:46 AM

Thu, Jul 26

andrew created D16462: Only use the default uart port on i386 and amd64..
Thu, Jul 26, 7:53 PM

Wed, Jul 25

andrew added inline comments to D16432: Use ACPI to probe serial devices & workaround limitations in acpi support.
Wed, Jul 25, 1:26 PM

Tue, Jul 24

andrew committed rS336677: icmp_quotelen was accidentially changes in r336676, undo this..
icmp_quotelen was accidentially changes in r336676, undo this.
Tue, Jul 24, 4:45 PM
andrew committed rS336676: Use the new VNET_DEFINE_STATIC macro when we are defining static VNET.
Use the new VNET_DEFINE_STATIC macro when we are defining static VNET
Tue, Jul 24, 4:36 PM
andrew committed rS336674: As with DPCPU create VNET_DEFINE_STATIC for when a variable needs to be.
As with DPCPU create VNET_DEFINE_STATIC for when a variable needs to be
Tue, Jul 24, 4:31 PM
andrew closed D16147: Create a macro for the static modifier with VNET.
Tue, Jul 24, 4:31 PM

Jul 20 2018

andrew added inline comments to D16147: Create a macro for the static modifier with VNET.
Jul 20 2018, 12:59 PM
andrew updated the diff for D16147: Create a macro for the static modifier with VNET.
  • Rebase
  • Update the man page (date will be changed when committed)
Jul 20 2018, 12:55 PM

Jul 19 2018

andrew committed rS336492: Stop writing past the end of the buffer in the msgget_limit test. The value.
Stop writing past the end of the buffer in the msgget_limit test. The value
Jul 19 2018, 5:14 PM
andrew created D16349: Set a mode when calling open with O_CREAT.
Jul 19 2018, 3:42 PM

Jul 18 2018

andrew committed rS336447: Also check if __ARM_ARCH_6KZ__ is defined when detecting when to use ARMv6.
Also check if __ARM_ARCH_6KZ__ is defined when detecting when to use ARMv6
Jul 18 2018, 9:17 AM
andrew added a comment to D16312: Remove Atmel AT91RM9200 and AT91SAM9 support..

I think this will also remove support for the last ARMv4 SoC.

Jul 18 2018, 9:04 AM
andrew added a comment to D16312: Remove Atmel AT91RM9200 and AT91SAM9 support..

I think this will also remove support for the last ARMv4 SoC.

Jul 18 2018, 8:39 AM

Jul 16 2018

andrew committed rS336349: Don't use the static keyword with DPCPU defines in arm64 modules..
Don't use the static keyword with DPCPU defines in arm64 modules.
Jul 16 2018, 6:21 PM
andrew closed D16145: Don't use static on DPCPU data in arm64 modules.
Jul 16 2018, 6:21 PM
andrew committed rS336348: Create an empty stdint.h for arm_neon.h to include..
Create an empty stdint.h for arm_neon.h to include.
Jul 16 2018, 3:39 PM
andrew closed D16254: Create an empty stdint.h for arm_neon.h to include..
Jul 16 2018, 3:39 PM
andrew updated the diff for D16145: Don't use static on DPCPU data in arm64 modules.

Update the comment.

Jul 16 2018, 3:20 PM
andrew added a comment to D16260: Use memory locality info provided in the FDT..
In D16260#345214, @alc wrote:

Does this architecture actually need VM_FREELIST_ISADMA?

From my reading of the code I don't think so, but I'm unsure it's intended purpose.

It ensures that the first 16MB of physical memory is segregated from the rest and won't be allocated by the generic page allocator unless nothing else is available. Allocations by drivers that need memory in that range are thus more likely to succeed.

Jul 16 2018, 2:46 PM
andrew added a comment to D16260: Use memory locality info provided in the FDT..

I've been thinking about replacing fdt_get_mem_region with fdt_foreach_mem_region to iterate over all memory regions and run a callback on each. It might pay to do this for get_mem_regions so we don't need to add a new fixed size struct fdt_mem_region array.

Jul 16 2018, 2:44 PM
andrew added a comment to D16260: Use memory locality info provided in the FDT..
In D16260#345214, @alc wrote:

Does this architecture actually need VM_FREELIST_ISADMA?

Jul 16 2018, 2:29 PM

Jul 13 2018

andrew accepted D16259: Fix vnic fallback PHY name matching after r334880..
Jul 13 2018, 10:33 PM
andrew accepted D16257: As discussed several times on freebsd-arch, start to decommission armeb..
Jul 13 2018, 5:27 PM
andrew created D16254: Create an empty stdint.h for arm_neon.h to include..
Jul 13 2018, 12:23 PM

Jul 6 2018

andrew committed rS336027: Teach binutils that arm64 is a 64bit architecture. This is needed to cross.
Teach binutils that arm64 is a 64bit architecture. This is needed to cross
Jul 6 2018, 11:51 AM
andrew accepted D15191: Export a breakpoint() function to userland..
Jul 6 2018, 11:40 AM

Jul 5 2018

andrew added a comment to D16147: Create a macro for the static modifier with VNET.

I still need to update vnet(9)

Jul 5 2018, 6:51 PM
andrew created D16147: Create a macro for the static modifier with VNET.
Jul 5 2018, 6:49 PM
andrew created D16145: Don't use static on DPCPU data in arm64 modules.
Jul 5 2018, 6:26 PM
andrew committed rS336007: Create a new macro for static DPCPU data..
Create a new macro for static DPCPU data.
Jul 5 2018, 5:13 PM
andrew closed D16140: Create a new macro for static DPCPU data.
Jul 5 2018, 5:13 PM
andrew added a comment to D16141: Disable sbrk() use in GNU tools..

I'm running a tinderbox on ref12-aarch64 with this and an unrelated patch to binutils to test cross building from arm64.

Jul 5 2018, 4:20 PM
andrew accepted D16141: Disable sbrk() use in GNU tools..
Jul 5 2018, 4:18 PM
andrew updated the diff for D16140: Create a new macro for static DPCPU data.

Add a comment on why struct _hack
Update the man page

Jul 5 2018, 4:18 PM
andrew updated the diff for D16140: Create a new macro for static DPCPU data.

Rename the static macro to DPCPU_DEFINE_STATIC
Keep DPCPU_DEFINE, but make it a compile time error to use it with static

Jul 5 2018, 3:33 PM
andrew added a reviewer for D16140: Create a new macro for static DPCPU data: manu.
Jul 5 2018, 1:54 PM
andrew edited reviewers for D16140: Create a new macro for static DPCPU data, added: bz; removed: manu.
Jul 5 2018, 1:54 PM
andrew created D16140: Create a new macro for static DPCPU data.
Jul 5 2018, 1:35 PM

Jul 3 2018

andrew added inline comments to D15933: Back pcpu zone with domain correct pages.
Jul 3 2018, 10:46 PM

Jul 2 2018

andrew added inline comments to D15933: Back pcpu zone with domain correct pages.
Jul 2 2018, 10:39 AM

Jun 25 2018

andrew committed rS335649: Make cpu_set_syscall_retval common between the existing FreeBSD ABI and.
Make cpu_set_syscall_retval common between the existing FreeBSD ABI and
Jun 25 2018, 10:36 PM
andrew closed D16008: Allow the linuxulator to use a common cpu_set_syscall_retval.
Jun 25 2018, 10:36 PM
andrew updated the diff for D16008: Allow the linuxulator to use a common cpu_set_syscall_retval.

Use td->td_frame

Jun 25 2018, 4:54 PM
andrew updated the diff for D16008: Allow the linuxulator to use a common cpu_set_syscall_retval.

Use the correct variable in the Linuxulator code

Jun 25 2018, 3:33 PM
andrew created D16008: Allow the linuxulator to use a common cpu_set_syscall_retval.
Jun 25 2018, 2:48 PM

Jun 22 2018

andrew updated the diff for D15819: Implement the SSBD (CVE-2018-3639) workaround on arm64.

Fix the SMCCC_ARCH_WORKAROUND_2 function ID

Jun 22 2018, 12:39 PM
andrew added inline comments to D15141: Add support for ThunderX2 PCIe.
Jun 22 2018, 12:14 PM
andrew added inline comments to D15929: Add quirk mechanism to pci_host_generic_acpi.
Jun 22 2018, 11:51 AM

Jun 21 2018

andrew added inline comments to D15929: Add quirk mechanism to pci_host_generic_acpi.
Jun 21 2018, 4:10 PM

Jun 20 2018

andrew added inline comments to D15929: Add quirk mechanism to pci_host_generic_acpi.
Jun 20 2018, 5:32 PM
andrew accepted D15928: Add ThunderX2 CPU revision macro. Add ThunderX2 name in identcpu.c.
Jun 20 2018, 5:16 PM
andrew committed rS335440: Move the SYSINIT to allow userspace access to the ARM generic timer later.
Move the SYSINIT to allow userspace access to the ARM generic timer later
Jun 20 2018, 11:13 AM
andrew committed rS335439: Move the SMCCC SYSINIT later in the boot so the psci driver has attached..
Move the SMCCC SYSINIT later in the boot so the psci driver has attached.
Jun 20 2018, 10:57 AM
andrew committed rS335438: Fix the SMCCC signatures, they are all 32-bit calls. This fixes SMCCC.
Fix the SMCCC signatures, they are all 32-bit calls. This fixes SMCCC
Jun 20 2018, 10:03 AM

Jun 19 2018

andrew added inline comments to D15141: Add support for ThunderX2 PCIe.
Jun 19 2018, 4:58 PM
andrew committed rS335373: Move common GIC interrupt numbers to the common header. These are the same.
Move common GIC interrupt numbers to the common header. These are the same
Jun 19 2018, 4:14 PM
andrew added inline comments to D15834: arm64 linuxulator: arm64 linux64 sysvec.
Jun 19 2018, 1:48 PM
andrew accepted D15834: arm64 linuxulator: arm64 linux64 sysvec.
Jun 19 2018, 8:10 AM

Jun 18 2018

andrew accepted D15832: Stub arm64 linuxulator routines.
Jun 18 2018, 5:06 PM