Release Cosmopolitan v3.6.0

This release is an atomic upgrade to GCC 14.1.0 with C23 and C++23

third_party/aarch64/acc_prof.internal.h

@@ -1,164 +0,0 @@
-#if defined(__aarch64__) && !(__ASSEMBLER__ + __LINKER__ + 0)
-#ifndef _ACC_PROF_H
-#define _ACC_PROF_H 1
-#include "third_party/aarch64/openacc.internal.h"
-#ifdef __cplusplus
-extern "C" {
-#endif
-typedef enum acc_event_t
-{
-  acc_ev_none = 0,
-  acc_ev_device_init_start,
-  acc_ev_device_init_end,
-  acc_ev_device_shutdown_start,
-  acc_ev_device_shutdown_end,
-  acc_ev_runtime_shutdown,
-  acc_ev_create,
-  acc_ev_delete,
-  acc_ev_alloc,
-  acc_ev_free,
-  acc_ev_enter_data_start,
-  acc_ev_enter_data_end,
-  acc_ev_exit_data_start,
-  acc_ev_exit_data_end,
-  acc_ev_update_start,
-  acc_ev_update_end,
-  acc_ev_compute_construct_start,
-  acc_ev_compute_construct_end,
-  acc_ev_enqueue_launch_start,
-  acc_ev_enqueue_launch_end,
-  acc_ev_enqueue_upload_start,
-  acc_ev_enqueue_upload_end,
-  acc_ev_enqueue_download_start,
-  acc_ev_enqueue_download_end,
-  acc_ev_wait_start,
-  acc_ev_wait_end,
-  acc_ev_last
-} acc_event_t;
-typedef signed long int _acc_prof_ssize_t;
-typedef unsigned long int _acc_prof_size_t;
-typedef int _acc_prof_int_t;
-#define _ACC_PROF_VALID_BYTES_STRUCT(_struct, _lastfield, _valid_bytes_lastfield) offsetof (_struct, _lastfield) + (_valid_bytes_lastfield)
-#if 0
-#define _ACC_PROF_VALID_BYTES_TYPE_N(_type, _n, _valid_bytes_type) ((_n - 1) * sizeof (_type) + (_valid_bytes_type))
-#endif
-#define _ACC_PROF_VALID_BYTES_BASICTYPE(_basictype) (sizeof (_basictype))
-typedef struct acc_prof_info
-{
-  acc_event_t event_type;
-  _acc_prof_int_t valid_bytes;
-  _acc_prof_int_t version;
-  acc_device_t device_type;
-  _acc_prof_int_t device_number;
-  _acc_prof_int_t thread_id;
-  _acc_prof_ssize_t async;
-  _acc_prof_ssize_t async_queue;
-  const char *src_file;
-  const char *func_name;
-  _acc_prof_int_t line_no, end_line_no;
-  _acc_prof_int_t func_line_no, func_end_line_no;
-#define _ACC_PROF_INFO_VALID_BYTES _ACC_PROF_VALID_BYTES_STRUCT (acc_prof_info, func_end_line_no, _ACC_PROF_VALID_BYTES_BASICTYPE (_acc_prof_int_t))
-} acc_prof_info;
-#define _ACC_PROF_INFO_VERSION 201711
-typedef enum acc_construct_t
-{
-  acc_construct_parallel = 0,
-  acc_construct_kernels,
-  acc_construct_loop,
-  acc_construct_data,
-  acc_construct_enter_data,
-  acc_construct_exit_data,
-  acc_construct_host_data,
-  acc_construct_atomic,
-  acc_construct_declare,
-  acc_construct_init,
-  acc_construct_shutdown,
-  acc_construct_set,
-  acc_construct_update,
-  acc_construct_routine,
-  acc_construct_wait,
-  acc_construct_runtime_api,
-  acc_construct_serial
-} acc_construct_t;
-typedef struct acc_data_event_info
-{
-  acc_event_t event_type;
-  _acc_prof_int_t valid_bytes;
-  acc_construct_t parent_construct;
-  _acc_prof_int_t implicit;
-  void *tool_info;
-  const char *var_name;
-  _acc_prof_size_t bytes;
-  const void *host_ptr;
-  const void *device_ptr;
-#define _ACC_DATA_EVENT_INFO_VALID_BYTES _ACC_PROF_VALID_BYTES_STRUCT (acc_data_event_info, device_ptr, _ACC_PROF_VALID_BYTES_BASICTYPE (void *))
-} acc_data_event_info;
-typedef struct acc_launch_event_info
-{
-  acc_event_t event_type;
-  _acc_prof_int_t valid_bytes;
-  acc_construct_t parent_construct;
-  _acc_prof_int_t implicit;
-  void *tool_info;
-  const char *kernel_name;
-  _acc_prof_size_t num_gangs, num_workers, vector_length;
-#define _ACC_LAUNCH_EVENT_INFO_VALID_BYTES _ACC_PROF_VALID_BYTES_STRUCT (acc_launch_event_info, vector_length, _ACC_PROF_VALID_BYTES_BASICTYPE (_acc_prof_size_t))
-} acc_launch_event_info;
-typedef struct acc_other_event_info
-{
-  acc_event_t event_type;
-  _acc_prof_int_t valid_bytes;
-  acc_construct_t parent_construct;
-  _acc_prof_int_t implicit;
-  void *tool_info;
-#define _ACC_OTHER_EVENT_INFO_VALID_BYTES _ACC_PROF_VALID_BYTES_STRUCT (acc_other_event_info, tool_info, _ACC_PROF_VALID_BYTES_BASICTYPE (void *))
-} acc_other_event_info;
-typedef union acc_event_info
-{
-  acc_event_t event_type;
-  acc_data_event_info data_event;
-  acc_launch_event_info launch_event;
-  acc_other_event_info other_event;
-} acc_event_info;
-typedef enum acc_device_api
-{
-  acc_device_api_none = 0,
-  acc_device_api_cuda,
-  acc_device_api_opencl,
-  acc_device_api_coi,
-  acc_device_api_other
-} acc_device_api;
-typedef struct acc_api_info
-{
-  acc_device_api device_api;
-  _acc_prof_int_t valid_bytes;
-  acc_device_t device_type;
-  _acc_prof_int_t vendor;
-  const void *device_handle;
-  const void *context_handle;
-  const void *async_handle;
-#define _ACC_API_INFO_VALID_BYTES _ACC_PROF_VALID_BYTES_STRUCT (acc_api_info, async_handle, _ACC_PROF_VALID_BYTES_BASICTYPE (void *))
-} acc_api_info;
-typedef void (*acc_prof_callback) (acc_prof_info *, acc_event_info *,
-       acc_api_info *);
-typedef enum acc_register_t
-{
-  acc_reg = 0,
-  acc_toggle = 1,
-  acc_toggle_per_thread = 2
-} acc_register_t;
-typedef void (*acc_prof_reg) (acc_event_t, acc_prof_callback, acc_register_t);
-extern void acc_prof_register (acc_event_t, acc_prof_callback,
-          acc_register_t) __GOACC_NOTHROW;
-extern void acc_prof_unregister (acc_event_t, acc_prof_callback,
-     acc_register_t) __GOACC_NOTHROW;
-typedef void (*acc_query_fn) ();
-typedef acc_query_fn (*acc_prof_lookup_func) (const char *);
-extern acc_query_fn acc_prof_lookup (const char *) __GOACC_NOTHROW;
-extern void acc_register_library (acc_prof_reg, acc_prof_reg,
-      acc_prof_lookup_func);
-#ifdef __cplusplus
-}
-#endif
-#endif
-#endif

third_party/aarch64/arm_acle.internal.h

@@ -27,6 +27,32 @@ _GCC_ARM_ACLE_DATA_FN (revsh, bswap16, int16_t, int16_t)
 _GCC_ARM_ACLE_DATA_FN (rev, bswap32, uint32_t, uint32_t)
 _GCC_ARM_ACLE_DATA_FN (revll, bswap64, uint64_t, uint64_t)
 #undef _GCC_ARM_ACLE_DATA_FN
+__extension__ extern __inline void
+__attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
+__pld (void const volatile *__addr)
+{
+  return __builtin_aarch64_pld (__addr);
+}
+__extension__ extern __inline void
+__attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
+__pli (void const volatile *__addr)
+{
+  return __builtin_aarch64_pli (__addr);
+}
+__extension__ extern __inline void
+__attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
+__plix (unsigned int __cache, unsigned int __rettn,
+ void const volatile *__addr)
+{
+  return __builtin_aarch64_plix (__cache, __rettn, __addr);
+}
+__extension__ extern __inline void
+__attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
+__pldx (unsigned int __access, unsigned int __cache, unsigned int __rettn,
+ void const volatile *__addr)
+{
+  return __builtin_aarch64_pldx (__access, __cache, __rettn, __addr);
+}
 __extension__ extern __inline unsigned long
 __attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
 __revl (unsigned long __value)
@@ -188,34 +214,7 @@ __ttest (void)
 #pragma GCC pop_options
 #endif
 #ifdef __ARM_FEATURE_LS64
-#pragma GCC push_options
-#pragma GCC target ("+nothing+ls64")
 typedef __arm_data512_t data512_t;
-__extension__ extern __inline data512_t
-__attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
-__arm_ld64b (const void *__addr)
-{
-  return __builtin_aarch64_ld64b (__addr);
-}
-__extension__ extern __inline void
-__attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
-__arm_st64b (void *__addr, data512_t __value)
-{
-  __builtin_aarch64_st64b (__addr, __value);
-}
-__extension__ extern __inline uint64_t
-__attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
-__arm_st64bv (void *__addr, data512_t __value)
-{
-  return __builtin_aarch64_st64bv (__addr, __value);
-}
-__extension__ extern __inline uint64_t
-__attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
-__arm_st64bv0 (void *__addr, data512_t __value)
-{
-  return __builtin_aarch64_st64bv0 (__addr, __value);
-}
-#pragma GCC pop_options
 #endif
 #pragma GCC push_options
 #pragma GCC target ("+nothing+rng")
@@ -233,7 +232,7 @@ __rndrrs (uint64_t *__res)
 }
 #pragma GCC pop_options
 #pragma GCC push_options
-#pragma GCC target ("arch=armv8.5-a+memtag")
+#pragma GCC target ("+nothing+memtag")
 #define __arm_mte_create_random_tag(__ptr, __u64_mask) __builtin_aarch64_memtag_irg(__ptr, __u64_mask)
 #define __arm_mte_exclude_tag(__ptr, __u64_excluded) __builtin_aarch64_memtag_gmi(__ptr, __u64_excluded)
 #define __arm_mte_ptrdiff(__ptr_a, __ptr_b) __builtin_aarch64_memtag_subp(__ptr_a, __ptr_b)
@@ -241,6 +240,21 @@ __rndrrs (uint64_t *__res)
 #define __arm_mte_set_tag(__tagged_address) __builtin_aarch64_memtag_set_tag(__tagged_address)
 #define __arm_mte_get_tag(__address) __builtin_aarch64_memtag_get_tag(__address)
 #pragma GCC pop_options
+#define __arm_rsr(__regname) __builtin_aarch64_rsr (__regname)
+#define __arm_rsrp(__regname) __builtin_aarch64_rsrp (__regname)
+#define __arm_rsr64(__regname) __builtin_aarch64_rsr64 (__regname)
+#define __arm_rsrf(__regname) __builtin_aarch64_rsrf (__regname)
+#define __arm_rsrf64(__regname) __builtin_aarch64_rsrf64 (__regname)
+#define __arm_wsr(__regname, __value) __builtin_aarch64_wsr (__regname, __value)
+#define __arm_wsrp(__regname, __value) __builtin_aarch64_wsrp (__regname, __value)
+#define __arm_wsr64(__regname, __value) __builtin_aarch64_wsr64 (__regname, __value)
+#define __arm_wsrf(__regname, __value) __builtin_aarch64_wsrf (__regname, __value)
+#define __arm_wsrf64(__regname, __value) __builtin_aarch64_wsrf64 (__regname, __value)
+#pragma GCC push_options
+#pragma GCC target ("+nothing+d128")
+#define __arm_rsr128(__regname) __builtin_aarch64_rsr128 (__regname)
+#define __arm_wsr128(__regname, __value) __builtin_aarch64_wsr128 (__regname, __value)
+#pragma GCC pop_options
 #ifdef __cplusplus
 }
 #endif

third_party/aarch64/arm_fp16.internal.h

@@ -2,7 +2,7 @@
 #ifndef _AARCH64_FP16_H_
 #define _AARCH64_FP16_H_
 #pragma GCC push_options
-#pragma GCC target ("arch=armv8.2-a+fp16")
+#pragma GCC target ("+nothing+fp16")
 typedef __fp16 float16_t;
 __extension__ extern __inline float16_t
 __attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
@@ -260,7 +260,7 @@ __extension__ extern __inline float16_t
 __attribute__ ((__always_inline__, __gnu_inline__, __artificial__))
 vnegh_f16 (float16_t __a)
 {
-  return __builtin_aarch64_neghf (__a);
+  return -__a;
 }
 __extension__ extern __inline float16_t
 __attribute__ ((__always_inline__, __gnu_inline__, __artificial__))

third_party/aarch64/openacc.internal.h

@@ -1,111 +0,0 @@
-#if defined(__aarch64__) && !(__ASSEMBLER__ + __LINKER__ + 0)
-#ifndef _OPENACC_H
-#define _OPENACC_H 1
-#ifdef __cplusplus
-extern "C" {
-#endif
-#if __cplusplus >= 201103
-# define __GOACC_NOTHROW noexcept
-#elif __cplusplus
-# define __GOACC_NOTHROW throw ()
-#else
-# define __GOACC_NOTHROW __attribute__ ((__nothrow__))
-#endif
-typedef enum acc_device_t {
-  acc_device_current = -1,
-  acc_device_none = 0,
-  acc_device_default = 1,
-  acc_device_host = 2,
-  acc_device_not_host = 4,
-  acc_device_nvidia = 5,
-  acc_device_radeon = 8,
-  _ACC_device_hwm,
-  _ACC_highest = __INT_MAX__,
-  _ACC_neg = -1
-} acc_device_t;
-typedef enum acc_device_property_t {
-  acc_property_memory = 1,
-  acc_property_free_memory = 2,
-  acc_property_name = 0x10001,
-  acc_property_vendor = 0x10002,
-  acc_property_driver = 0x10003
-} acc_device_property_t;
-typedef enum acc_async_t {
-  acc_async_noval = -1,
-  acc_async_sync = -2
-} acc_async_t;
-int acc_get_num_devices (acc_device_t) __GOACC_NOTHROW;
-void acc_set_device_type (acc_device_t) __GOACC_NOTHROW;
-acc_device_t acc_get_device_type (void) __GOACC_NOTHROW;
-void acc_set_device_num (int, acc_device_t) __GOACC_NOTHROW;
-int acc_get_device_num (acc_device_t) __GOACC_NOTHROW;
-size_t acc_get_property
-  (int, acc_device_t, acc_device_property_t) __GOACC_NOTHROW;
-const char *acc_get_property_string
-  (int, acc_device_t, acc_device_property_t) __GOACC_NOTHROW;
-int acc_async_test (int) __GOACC_NOTHROW;
-int acc_async_test_all (void) __GOACC_NOTHROW;
-void acc_wait (int) __GOACC_NOTHROW;
-void acc_async_wait (int) __GOACC_NOTHROW;
-void acc_wait_async (int, int) __GOACC_NOTHROW;
-void acc_wait_all (void) __GOACC_NOTHROW;
-void acc_async_wait_all (void) __GOACC_NOTHROW;
-void acc_wait_all_async (int) __GOACC_NOTHROW;
-void acc_init (acc_device_t) __GOACC_NOTHROW;
-void acc_shutdown (acc_device_t) __GOACC_NOTHROW;
-#ifdef __cplusplus
-int acc_on_device (int __arg) __GOACC_NOTHROW;
-#else
-int acc_on_device (acc_device_t __arg) __GOACC_NOTHROW;
-#endif
-void *acc_malloc (size_t) __GOACC_NOTHROW;
-void acc_free (void *) __GOACC_NOTHROW;
-void *acc_copyin (void *, size_t) __GOACC_NOTHROW;
-void *acc_present_or_copyin (void *, size_t) __GOACC_NOTHROW;
-void *acc_pcopyin (void *, size_t) __GOACC_NOTHROW;
-void *acc_create (void *, size_t) __GOACC_NOTHROW;
-void *acc_present_or_create (void *, size_t) __GOACC_NOTHROW;
-void *acc_pcreate (void *, size_t) __GOACC_NOTHROW;
-void acc_copyout (void *, size_t) __GOACC_NOTHROW;
-void acc_delete (void *, size_t) __GOACC_NOTHROW;
-void acc_update_device (void *, size_t) __GOACC_NOTHROW;
-void acc_update_self (void *, size_t) __GOACC_NOTHROW;
-void acc_map_data (void *, void *, size_t) __GOACC_NOTHROW;
-void acc_unmap_data (void *) __GOACC_NOTHROW;
-void *acc_deviceptr (void *) __GOACC_NOTHROW;
-void *acc_hostptr (void *) __GOACC_NOTHROW;
-int acc_is_present (void *, size_t) __GOACC_NOTHROW;
-void acc_memcpy_to_device (void *, void *, size_t) __GOACC_NOTHROW;
-void acc_memcpy_from_device (void *, void *, size_t) __GOACC_NOTHROW;
-void acc_attach (void **) __GOACC_NOTHROW;
-void acc_attach_async (void **, int) __GOACC_NOTHROW;
-void acc_detach (void **) __GOACC_NOTHROW;
-void acc_detach_async (void **, int) __GOACC_NOTHROW;
-void acc_copyout_finalize (void *, size_t) __GOACC_NOTHROW;
-void acc_copyout_finalize_async (void *, size_t, int) __GOACC_NOTHROW;
-void acc_delete_finalize (void *, size_t) __GOACC_NOTHROW;
-void acc_delete_finalize_async (void *, size_t, int) __GOACC_NOTHROW;
-void acc_detach_finalize (void **) __GOACC_NOTHROW;
-void acc_detach_finalize_async (void **, int) __GOACC_NOTHROW;
-void acc_copyin_async (void *, size_t, int) __GOACC_NOTHROW;
-void acc_create_async (void *, size_t, int) __GOACC_NOTHROW;
-void acc_copyout_async (void *, size_t, int) __GOACC_NOTHROW;
-void acc_delete_async (void *, size_t, int) __GOACC_NOTHROW;
-void acc_update_device_async (void *, size_t, int) __GOACC_NOTHROW;
-void acc_update_self_async (void *, size_t, int) __GOACC_NOTHROW;
-void acc_memcpy_to_device_async (void *, void *, size_t, int) __GOACC_NOTHROW;
-void acc_memcpy_from_device_async (void *, void *, size_t, int) __GOACC_NOTHROW;
-void *acc_get_current_cuda_device (void) __GOACC_NOTHROW;
-void *acc_get_current_cuda_context (void) __GOACC_NOTHROW;
-void *acc_get_cuda_stream (int) __GOACC_NOTHROW;
-int acc_set_cuda_stream (int, void *) __GOACC_NOTHROW;
-#ifdef __cplusplus
-}
-#pragma acc routine seq
-inline int acc_on_device (acc_device_t __arg) __GOACC_NOTHROW
-{
-  return acc_on_device ((int) __arg);
-}
-#endif
-#endif
-#endif

third_party/aarch64/upgrade.sh

@@ -13,17 +13,15 @@
 # 3. You should fix up the `#pragma GCC aarch64` things.
 #
 
-s=/opt/goodies/include
+s=/opt/include
 d=third_party/aarch64
 
 FILES='
-acc_prof
 arm_acle
 arm_bf16
 arm_fp16
 arm_neon
 arm_sve
-openacc
 '
 
 strip_c_comments() {