Fix the behavior of redbean -i -e CODE

When redbean is functioning as a Lua interpreter, the `-e` flag should
behave the same way as other open source language interpreters. Namely
it should exit after evaluating the code rather than showing the REPL.

.gitignore

@@ -1,7 +1,6 @@
 # -*- conf -*-
 
 /o
-/.prompt.jtlp
 
 # TODO: Find some way to have Python write to o/
 __pycache__

Makefile

@@ -143,9 +143,7 @@ include libc/time/time.mk			# │
 include libc/stdio/stdio.mk			# │
 include third_party/libcxx/libcxx.mk		# │
 include net/net.mk				# │
-include third_party/vqsort/vqsort.mk		# │
 include libc/log/log.mk				# │
-include third_party/ggml/ggml.mk		# │
 include third_party/bzip2/bzip2.mk		# │
 include dsp/core/core.mk			# │
 include libc/x/x.mk				# │
@@ -155,7 +153,6 @@ include dsp/mpeg/mpeg.mk			# │
 include dsp/dsp.mk				# │
 include third_party/zlib/gz/gz.mk		# │
 include third_party/musl/musl.mk		# │
-include third_party/intel/intel.mk		# │
 include libc/libc.mk				#─┘
 include libc/sock/sock.mk			#─┐
 include dsp/tty/tty.mk				# ├──ONLINE RUNTIME
@@ -417,8 +414,7 @@ toolchain:	o/cosmopolitan.h				\
 		o/$(MODE)/ape/ape.o				\
 		o/$(MODE)/ape/ape-copy-self.o			\
 		o/$(MODE)/ape/ape-no-modify-self.o		\
-		o/$(MODE)/cosmopolitan.a			\
-		o/$(MODE)/third_party/libcxx/libcxx.a
+		o/$(MODE)/cosmopolitan.a
 
 # UNSPECIFIED PREREQUISITES TUTORIAL
 #

dsp/tty/internal.h

@@ -1,7 +1,7 @@
 #ifndef COSMOPOLITAN_DSP_TTY_INTERNAL_H_
 #define COSMOPOLITAN_DSP_TTY_INTERNAL_H_
 #include "dsp/tty/ttyrgb.h"
-#include "third_party/intel/xmmintrin.internal.h"
+#include "libc/intrin/xmmintrin.internal.h"
 #if !(__ASSEMBLER__ + __LINKER__ + 0)
 COSMOPOLITAN_C_START_
 

dsp/tty/quant.h

@@ -3,9 +3,9 @@
 #include "dsp/tty/ttyrgb.h"
 #include "libc/assert.h"
 #include "libc/intrin/bits.h"
+#include "libc/intrin/xmmintrin.internal.h"
 #include "libc/limits.h"
 #include "libc/str/str.h"
-#include "third_party/intel/xmmintrin.internal.h"
 #if !(__ASSEMBLER__ + __LINKER__ + 0)
 COSMOPOLITAN_C_START_
 

dsp/tty/rgb2ttyf2i.c

@@ -17,7 +17,7 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "dsp/tty/quant.h"
-#include "third_party/intel/xmmintrin.internal.h"
+#include "libc/intrin/xmmintrin.internal.h"
 
 struct TtyRgb rgb2ttyf2i_(__m128 rgb) {
   __v4si i4;

examples/examples.mk

@@ -89,7 +89,6 @@ EXAMPLES_DIRECTDEPS =								\
 	THIRD_PARTY_SED								\
 	THIRD_PARTY_STB								\
 	THIRD_PARTY_TR								\
-	THIRD_PARTY_VQSORT							\
 	THIRD_PARTY_XED								\
 	THIRD_PARTY_ZLIB							\
 	TOOL_BUILD_LIB								\

examples/vqsort.c

@@ -1,25 +0,0 @@
-#if 0
-/*─────────────────────────────────────────────────────────────────╗
-│ To the extent possible under law, Justine Tunney has waived      │
-│ all copyright and related or neighboring rights to this file,    │
-│ as it is written in the following disclaimers:                   │
-│   • http://unlicense.org/                                        │
-│   • http://creativecommons.org/publicdomain/zero/1.0/            │
-╚─────────────────────────────────────────────────────────────────*/
-#endif
-#include "third_party/vqsort/vqsort.h"
-#include "libc/macros.internal.h"
-#include "libc/stdio/stdio.h"
-#include "third_party/vqsort/vqsort.h"
-
-// how to sort one gigabyte of 64-bit integers per second
-
-int main(int argc, char *argv[]) {
-  int64_t A[] = {9, 3, -3, 5, 23, 7};
-  vqsort_int64(A, ARRAYLEN(A));
-  for (int i = 0; i < ARRAYLEN(A); ++i) {
-    if (i) printf(" ");
-    printf("%ld", A[i]);
-  }
-  printf("\n");
-}

libc/calls/calls.h

@@ -23,7 +23,6 @@
 #define _POSIX_READER_WRITER_LOCKS        _POSIX_VERSION
 #define _POSIX_SEMAPHORES                 _POSIX_VERSION
 #define _POSIX_SHARED_MEMORY_OBJECTS      _POSIX_VERSION
-#define _POSIX_MEMLOCK_RANGE              _POSIX_VERSION
 
 #define EOF      -1         /* end of file */
 #define WEOF     -1u        /* end of file (multibyte) */

libc/calls/clock.c

@@ -16,11 +16,11 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/sysv/consts/clock.h"
 #include "libc/calls/struct/rusage.h"
 #include "libc/calls/struct/timespec.h"
 #include "libc/calls/struct/timeval.h"
 #include "libc/errno.h"
+#include "libc/sysv/consts/clock.h"
 #include "libc/sysv/consts/rusage.h"
 #include "libc/time/time.h"
 

libc/calls/copyfile.c

@@ -16,8 +16,8 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/copyfile.h"
 #include "libc/calls/calls.h"
+#include "libc/calls/copyfile.h"
 #include "libc/calls/struct/stat.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/dce.h"

libc/calls/fchown.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/sysv/consts/at.h"
 
 /**

libc/calls/getdomainname.c

@@ -17,10 +17,10 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-sysv.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/kprintf.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/macros.internal.h"
 #include "libc/nt/enum/computernameformat.h"
 #include "libc/str/str.h"

libc/calls/gethostname.c

@@ -17,10 +17,10 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-sysv.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/kprintf.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/enum/computernameformat.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/getitimer.c

@@ -17,11 +17,11 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/struct/itimerval.h"
 #include "libc/calls/struct/itimerval.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/asan.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/errfuns.h"
 
 /**

libc/calls/getpgid.c

@@ -17,9 +17,9 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
-#include "libc/intrin/strace.internal.h"
 
 /**
  * Returns process group id.

libc/calls/getresgid.c

@@ -17,9 +17,9 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
-#include "libc/intrin/strace.internal.h"
 
 /**
  * Gets real, effective, and "saved" group ids.

libc/calls/getresuid.c

@@ -17,9 +17,9 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
-#include "libc/intrin/strace.internal.h"
 
 /**
  * Gets real, effective, and "saved" user ids.

libc/calls/getrlimit.c

@@ -17,11 +17,11 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/struct/rlimit.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/asan.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/rlimit.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/getrusage.c

@@ -17,11 +17,11 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/struct/rusage.h"
 #include "libc/calls/struct/rusage.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/asan.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/errfuns.h"
 
 /**

libc/calls/getsid.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Creates session and sets the process group id.

libc/calls/ioctl_fioclex.c

@@ -18,9 +18,9 @@
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/internal.h"
 #include "libc/calls/ioctl.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/o.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/ioctl_tcsets-nt.c

@@ -17,10 +17,10 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/internal.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/struct/metatermios.internal.h"
 #include "libc/calls/termios.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/console.h"
 #include "libc/nt/enum/consolemodeflags.h"
 #include "libc/nt/enum/version.h"

libc/calls/ioctl_tiocgwinsz.c

@@ -18,12 +18,12 @@
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/internal.h"
 #include "libc/calls/ioctl.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/struct/winsize.h"
 #include "libc/calls/struct/winsize.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/asan.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/termios.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/isatty.c

@@ -18,12 +18,12 @@
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
 #include "libc/calls/internal.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/struct/winsize.h"
 #include "libc/calls/syscall-nt.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/calls/syscall_support-sysv.internal.h"
 #include "libc/errno.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/termios.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/issetugid.c

@@ -16,11 +16,11 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/_getauxval.internal.h"
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
-#include "libc/intrin/_getauxval.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/auxv.h"
 
 /**

libc/calls/landlock.h

@@ -29,8 +29,7 @@
 /**
  * Control file truncation.
  *
- * @see
- * https://lore.kernel.org/all/[email protected]/
+ * @see https://lore.kernel.org/all/[email protected]/
  * @see https://docs.kernel.org/userspace-api/landlock.html
  * @note ABI 3+
  */

libc/calls/madvise.c

@@ -17,11 +17,11 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall-nt.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/asan.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/errfuns.h"
 
 /**

libc/calls/memfd_create.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Creates anonymous file.

libc/calls/mincore.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Tells you which pages are resident in memory.

libc/calls/mkntpathat.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/internal.h"
-#include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/macros.internal.h"
 #include "libc/nt/files.h"
 #include "libc/str/str.h"

libc/calls/mremap-sysv.greg.c

@@ -17,10 +17,10 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/dce.h"
 #include "libc/errno.h"
 #include "libc/intrin/asmflag.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/map.h"
 #include "libc/sysv/consts/mremap.h"
 #include "libc/sysv/errfuns.h"

libc/calls/munlock.c

@@ -1,44 +0,0 @@
-/*-*- mode:c;indent-tabs-mode:nil;c-basic-offset:2;tab-width:8;coding:utf-8 -*-│
-│vi: set net ft=c ts=2 sts=2 sw=2 fenc=utf-8                                :vi│
-╞══════════════════════════════════════════════════════════════════════════════╡
-│ Copyright 2023 Justine Alexandra Roberts Tunney                              │
-│                                                                              │
-│ Permission to use, copy, modify, and/or distribute this software for         │
-│ any purpose with or without fee is hereby granted, provided that the         │
-│ above copyright notice and this permission notice appear in all copies.      │
-│                                                                              │
-│ THE SOFTWARE IS PROVIDED "AS IS" AND THE AUTHOR DISCLAIMS ALL                │
-│ WARRANTIES WITH REGARD TO THIS SOFTWARE INCLUDING ALL IMPLIED                │
-│ WARRANTIES OF MERCHANTABILITY AND FITNESS. IN NO EVENT SHALL THE             │
-│ AUTHOR BE LIABLE FOR ANY SPECIAL, DIRECT, INDIRECT, OR CONSEQUENTIAL         │
-│ DAMAGES OR ANY DAMAGES WHATSOEVER RESULTING FROM LOSS OF USE, DATA OR        │
-│ PROFITS, WHETHER IN AN ACTION OF CONTRACT, NEGLIGENCE OR OTHER               │
-│ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
-│ PERFORMANCE OF THIS SOFTWARE.                                                │
-╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/calls.h"
-#include "libc/calls/syscall_support-nt.internal.h"
-#include "libc/dce.h"
-#include "libc/nt/memory.h"
-#include "libc/runtime/runtime.h"
-
-static textwindows int sys_munlock_nt(const void *addr, size_t len) {
-  if (VirtualUnlock(addr, len)) {
-    return 0;
-  } else {
-    return __winerr();
-  }
-}
-
-/**
- * Unlocks virtual memory interval from RAM, to permit swapping.
- *
- * @return 0 on success, or -1 w/ errno
- */
-int munlock(const void *addr, size_t len) {
-  if (!IsWindows()) {
-    return sys_munlock(addr, len);
-  } else {
-    return sys_munlock_nt(addr, len);
-  }
-}

libc/calls/openat-metal.c

@@ -40,13 +40,14 @@ int sys_openat_metal(int dirfd, const char *file, int flags, unsigned mode) {
   struct MetalFile *state;
   if (dirfd != AT_FDCWD || strcmp(file, APE_COM_NAME)) return enoent();
   if (flags != O_RDONLY) return eacces();
-  if (!_weaken(__ape_com_base) || !_weaken(__ape_com_size)) return eopnotsupp();
+  if (!_weaken(__ape_com_base) || !_weaken(__ape_com_size))
+    return eopnotsupp();
   if ((fd = __reservefd(-1)) == -1) return -1;
   if (!_weaken(calloc) || !_weaken(free)) {
     struct DirectMap dm;
     dm = sys_mmap_metal(NULL, ROUNDUP(sizeof(struct MetalFile), 4096),
-                        PROT_READ | PROT_WRITE, MAP_SHARED | MAP_ANONYMOUS, -1,
-                        0);
+                        PROT_READ | PROT_WRITE, MAP_SHARED | MAP_ANONYMOUS,
+                        -1, 0);
     state = dm.addr;
     if (state == (void *)-1) return -1;
   } else {

libc/calls/pivot_root.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Changes root mount.

libc/calls/prctl.c

@@ -17,10 +17,10 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/dce.h"
 #include "libc/errno.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/pr.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/ptrace.c

@@ -16,11 +16,11 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/sysv/consts/ptrace.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
+#include "libc/sysv/consts/ptrace.h"
 #include "libc/sysv/errfuns.h"
 
 /**

libc/calls/sched_get_priority_max.c

@@ -18,9 +18,9 @@
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
 #include "libc/calls/sched-sysv.internal.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/sched.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/sched_get_priority_min.c

@@ -18,9 +18,9 @@
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
 #include "libc/calls/sched-sysv.internal.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/sched.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/seccomp.c

@@ -16,12 +16,12 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/struct/seccomp.h"
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
+#include "libc/calls/struct/seccomp.h"
 #include "libc/dce.h"
 #include "libc/errno.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/sysv/consts/pr.h"
 #include "libc/sysv/errfuns.h"
 

libc/calls/setregid.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Sets real and/or effective group ids.

libc/calls/setresgid.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Sets real, effective, and "saved" group ids.

libc/calls/setresuid.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Sets real, effective, and "saved" user ids.

libc/calls/setreuid.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Sets real and/or effective user ids.

libc/calls/setsid.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Creates session and sets the process group id.

libc/calls/sigaction.c

@@ -16,13 +16,13 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/struct/sigaction.h"
 #include "libc/assert.h"
 #include "libc/calls/blocksigs.internal.h"
 #include "libc/calls/calls.h"
 #include "libc/calls/internal.h"
 #include "libc/calls/sig.internal.h"
 #include "libc/calls/state.internal.h"
+#include "libc/calls/struct/sigaction.h"
 #include "libc/calls/struct/sigaction.internal.h"
 #include "libc/calls/struct/siginfo.internal.h"
 #include "libc/calls/struct/sigset.h"
@@ -248,9 +248,8 @@ static int __sigaction(int sig, const struct sigaction *act,
   if (rc != -1 && !__vforked) {
     if (oldact) {
       oldrva = __sighandrvas[sig];
-      oldact->sa_sigaction =
-          (sigaction_f)(oldrva < kSigactionMinRva ? oldrva
-                                                  : (intptr_t)&_base + oldrva);
+      oldact->sa_sigaction = (sigaction_f)(
+          oldrva < kSigactionMinRva ? oldrva : (intptr_t)&_base + oldrva);
     }
     if (act) {
       __sighandrvas[sig] = rva;

libc/calls/sigaltstack.c

@@ -16,8 +16,8 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/struct/sigaltstack.h"
 #include "libc/calls/struct/metasigaltstack.h"
+#include "libc/calls/struct/sigaltstack.h"
 #include "libc/calls/struct/sigaltstack.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"

libc/calls/sigtimedwait.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/sigtimedwait.h"
 #include "libc/calls/asan.internal.h"
 #include "libc/calls/cp.internal.h"
+#include "libc/calls/sigtimedwait.h"
 #include "libc/calls/sigtimedwait.internal.h"
 #include "libc/calls/struct/siginfo.internal.h"
 #include "libc/calls/struct/sigset.internal.h"

libc/calls/statvfs.c

@@ -16,10 +16,10 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/struct/statvfs.h"
 #include "libc/calls/calls.h"
 #include "libc/calls/struct/statfs.h"
 #include "libc/calls/struct/statfs.internal.h"
+#include "libc/calls/struct/statvfs.h"
 
 /**
  * Returns information about filesystem.

libc/calls/symlinkat-nt.c

@@ -19,6 +19,7 @@
 #include "libc/calls/calls.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/errno.h"
+#include "libc/thread/thread.h"
 #include "libc/nt/enum/accessmask.h"
 #include "libc/nt/enum/fileflagandattributes.h"
 #include "libc/nt/enum/symboliclink.h"
@@ -31,7 +32,6 @@
 #include "libc/nt/struct/tokenprivileges.h"
 #include "libc/nt/thunk/msabi.h"
 #include "libc/sysv/errfuns.h"
-#include "libc/thread/thread.h"
 
 __msabi extern typeof(GetFileAttributes) *const __imp_GetFileAttributesW;
 

libc/calls/sync.c

@@ -17,10 +17,10 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall-nt.internal.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
-#include "libc/intrin/strace.internal.h"
 
 /**
  * Flushes file system changes to disk by any means necessary.

libc/calls/syscall-nt.internal.h

@@ -26,8 +26,7 @@ int sys_linkat_nt(int, const char *, int, const char *) _Hide;
 int sys_madvise_nt(void *, size_t, int) _Hide;
 int sys_mkdirat_nt(int, const char *, uint32_t) _Hide;
 int sys_msync_nt(char *, size_t, int) _Hide;
-int sys_open_nt(int, const char *, uint32_t, int32_t)
-dontdiscard _Hide;
+int sys_open_nt(int, const char *, uint32_t, int32_t) dontdiscard _Hide;
 int sys_pipe_nt(int[hasatleast 2], unsigned) _Hide;
 int sys_renameat_nt(int, const char *, int, const char *) _Hide;
 int sys_sched_yield_nt(void) _Hide;

libc/calls/sysinfo.c

@@ -16,8 +16,8 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/struct/sysinfo.h"
 #include "libc/calls/calls.h"
+#include "libc/calls/struct/sysinfo.h"
 #include "libc/calls/struct/sysinfo.internal.h"
 #include "libc/calls/struct/timespec.h"
 #include "libc/calls/struct/timeval.h"

libc/calls/time.c

@@ -16,11 +16,11 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/time/time.h"
 #include "libc/calls/struct/timeval.h"
 #include "libc/dce.h"
 #include "libc/intrin/asan.internal.h"
 #include "libc/sysv/errfuns.h"
+#include "libc/time/time.h"
 
 /**
  * Returns time as seconds from UNIX epoch.

libc/calls/ttyname_r.c

@@ -19,13 +19,13 @@
 #include "libc/assert.h"
 #include "libc/calls/calls.h"
 #include "libc/calls/internal.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/struct/stat.h"
 #include "libc/calls/syscall-sysv.internal.h"
 #include "libc/dce.h"
 #include "libc/errno.h"
 #include "libc/fmt/fmt.h"
 #include "libc/fmt/itoa.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/log/log.h"
 #include "libc/nt/console.h"
 #include "libc/nt/enum/consolemodeflags.h"

libc/calls/unmount.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/mount.h"
-#include "libc/calls/syscall-sysv.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall-sysv.internal.h"
 
 /**
  * Unmounts file system.

libc/calls/unveil.c

@@ -53,9 +53,8 @@
 #define UNVEIL_READ                                             \
   (LANDLOCK_ACCESS_FS_READ_FILE | LANDLOCK_ACCESS_FS_READ_DIR | \
    LANDLOCK_ACCESS_FS_REFER)
-#define UNVEIL_WRITE \
-  (LANDLOCK_ACCESS_FS_WRITE_FILE | LANDLOCK_ACCESS_FS_TRUNCATE)
-#define UNVEIL_EXEC (LANDLOCK_ACCESS_FS_EXECUTE)
+#define UNVEIL_WRITE (LANDLOCK_ACCESS_FS_WRITE_FILE | LANDLOCK_ACCESS_FS_TRUNCATE)
+#define UNVEIL_EXEC  (LANDLOCK_ACCESS_FS_EXECUTE)
 #define UNVEIL_CREATE                                             \
   (LANDLOCK_ACCESS_FS_MAKE_CHAR | LANDLOCK_ACCESS_FS_MAKE_DIR |   \
    LANDLOCK_ACCESS_FS_MAKE_REG | LANDLOCK_ACCESS_FS_MAKE_SOCK |   \
@@ -90,8 +89,7 @@ static const struct sock_filter kUnveilBlacklistLatestAbi[] = {
 static int landlock_abi_version;
 
 __attribute__((__constructor__)) void init_landlock_version() {
-  landlock_abi_version =
-      landlock_create_ruleset(0, 0, LANDLOCK_CREATE_RULESET_VERSION);
+  landlock_abi_version = landlock_create_ruleset(0, 0, LANDLOCK_CREATE_RULESET_VERSION);
 }
 
 /**
@@ -119,8 +117,8 @@ static int unveil_final(void) {
   };
   if (landlock_abi_version < 3) {
     sandbox = (struct sock_fprog){
-        .filter = kUnveilBlacklistAbiVersionBelow3,
-        .len = ARRAYLEN(kUnveilBlacklistAbiVersionBelow3),
+      .filter = kUnveilBlacklistAbiVersionBelow3,
+      .len = ARRAYLEN(kUnveilBlacklistAbiVersionBelow3),
     };
   }
   e = errno;

libc/calls/vdsofunc.greg.c

@@ -17,6 +17,7 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/elf/scalar.h"
 #include "libc/elf/struct/ehdr.h"
 #include "libc/elf/struct/phdr.h"
@@ -25,7 +26,6 @@
 #include "libc/elf/struct/verdaux.h"
 #include "libc/elf/struct/verdef.h"
 #include "libc/intrin/bits.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/runtime/runtime.h"
 #include "libc/sysv/consts/auxv.h"
 

libc/calls/wait4.c

@@ -16,10 +16,10 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/wait4.h"
 #include "libc/calls/calls.h"
 #include "libc/calls/cp.internal.h"
 #include "libc/calls/struct/rusage.internal.h"
+#include "libc/calls/wait4.h"
 #include "libc/dce.h"
 #include "libc/intrin/asan.internal.h"
 #include "libc/intrin/strace.internal.h"

libc/calls/weirdtypes.h

@@ -29,9 +29,9 @@
 #define sa_family_t   uint16_t /* bsd:uint8_t */
 #define socklen_t     uint32_t
 #define speed_t       uint32_t
-#define suseconds_t   int64_t  /* int32_t on xnu */
+#define suseconds_t   int64_t /* int32_t on xnu */
 #define useconds_t    uint64_t /* uint32_t on xnu */
-#define syscall_arg_t int64_t  /* uint64_t on xnu */
+#define syscall_arg_t int64_t /* uint64_t on xnu */
 #define tcflag_t      uint32_t
 #define time_t        int64_t
 #define timer_t       void*

libc/dns/dnsheader.c

@@ -16,8 +16,8 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/dns/dnsheader.h"
 #include "libc/intrin/bits.h"
+#include "libc/dns/dnsheader.h"
 #include "libc/sysv/errfuns.h"
 
 /**

libc/dns/getaddrinfo.c

@@ -16,15 +16,15 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/safemacros.internal.h"
 #include "libc/calls/calls.h"
 #include "libc/dns/dns.h"
 #include "libc/dns/hoststxt.h"
 #include "libc/dns/resolvconf.h"
 #include "libc/dns/servicestxt.h"
 #include "libc/fmt/conv.h"
-#include "libc/intrin/safemacros.internal.h"
-#include "libc/mem/gc.h"
 #include "libc/mem/mem.h"
+#include "libc/mem/gc.h"
 #include "libc/sock/sock.h"
 #include "libc/str/str.h"
 #include "libc/sysv/consts/af.h"

libc/dns/gethoststxt.c

@@ -16,19 +16,19 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/bits.h"
+#include "libc/intrin/pushpop.h"
+#include "libc/intrin/safemacros.internal.h"
 #include "libc/calls/calls.h"
 #include "libc/dce.h"
 #include "libc/dns/hoststxt.h"
 #include "libc/fmt/fmt.h"
-#include "libc/intrin/bits.h"
-#include "libc/intrin/pushpop.h"
-#include "libc/intrin/safemacros.internal.h"
+#include "libc/thread/thread.h"
 #include "libc/macros.internal.h"
 #include "libc/nt/systeminfo.h"
 #include "libc/runtime/runtime.h"
 #include "libc/stdio/stdio.h"
 #include "libc/str/str.h"
-#include "libc/thread/thread.h"
 
 static struct HostsTxt *g_hoststxt;
 static struct HostsTxtInitialStaticMemory {

libc/dns/getnameinfo.c

@@ -24,6 +24,7 @@
 │ ARISING FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR        │
 │ OTHER DEALINGS IN THE SOFTWARE.                                              │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/safemacros.internal.h"
 #include "libc/calls/calls.h"
 #include "libc/dns/consts.h"
 #include "libc/dns/dns.h"
@@ -33,7 +34,6 @@
 #include "libc/fmt/conv.h"
 #include "libc/fmt/fmt.h"
 #include "libc/fmt/itoa.h"
-#include "libc/intrin/safemacros.internal.h"
 #include "libc/mem/mem.h"
 #include "libc/sock/sock.h"
 #include "libc/str/str.h"

libc/dns/getresolvconf.c

@@ -16,16 +16,16 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/pushpop.h"
 #include "libc/dce.h"
 #include "libc/dns/resolvconf.h"
 #include "libc/fmt/fmt.h"
-#include "libc/intrin/pushpop.h"
+#include "libc/thread/thread.h"
 #include "libc/macros.internal.h"
 #include "libc/runtime/runtime.h"
 #include "libc/sock/sock.h"
 #include "libc/sock/struct/sockaddr.h"
 #include "libc/stdio/stdio.h"
-#include "libc/thread/thread.h"
 
 static struct ResolvConf *g_resolvconf;
 static struct ResolvConfInitialStaticMemory {

libc/dns/lookupprotobyname.c

@@ -24,11 +24,11 @@
 │ ARISING FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR        │
 │ OTHER DEALINGS IN THE SOFTWARE.                                              │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/safemacros.internal.h"
 #include "libc/dce.h"
 #include "libc/dns/prototxt.h"
 #include "libc/errno.h"
 #include "libc/fmt/conv.h"
-#include "libc/intrin/safemacros.internal.h"
 #include "libc/macros.internal.h"
 #include "libc/mem/mem.h"
 #include "libc/str/str.h"

libc/dns/lookupprotobynumber.c

@@ -24,11 +24,11 @@
 │ ARISING FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR        │
 │ OTHER DEALINGS IN THE SOFTWARE.                                              │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/safemacros.internal.h"
 #include "libc/dce.h"
 #include "libc/dns/prototxt.h"
 #include "libc/errno.h"
 #include "libc/fmt/conv.h"
-#include "libc/intrin/safemacros.internal.h"
 #include "libc/macros.internal.h"
 #include "libc/mem/mem.h"
 #include "libc/str/str.h"

libc/dns/lookupservicesbyname.c

@@ -24,11 +24,11 @@
 │ ARISING FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR        │
 │ OTHER DEALINGS IN THE SOFTWARE.                                              │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/safemacros.internal.h"
 #include "libc/dce.h"
 #include "libc/dns/servicestxt.h"
 #include "libc/errno.h"
 #include "libc/fmt/conv.h"
-#include "libc/intrin/safemacros.internal.h"
 #include "libc/macros.internal.h"
 #include "libc/mem/mem.h"
 #include "libc/str/str.h"

libc/dns/lookupservicesbyport.c

@@ -24,11 +24,11 @@
 │ ARISING FROM, OUT OF OR IN CONNECTION WITH THE SOFTWARE OR THE USE OR        │
 │ OTHER DEALINGS IN THE SOFTWARE.                                              │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/safemacros.internal.h"
 #include "libc/dce.h"
 #include "libc/dns/servicestxt.h"
 #include "libc/errno.h"
 #include "libc/fmt/conv.h"
-#include "libc/intrin/safemacros.internal.h"
 #include "libc/macros.internal.h"
 #include "libc/mem/mem.h"
 #include "libc/str/str.h"

libc/dns/parsehoststxt.c

@@ -16,10 +16,10 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/mem/arraylist.internal.h"
 #include "libc/dns/dns.h"
 #include "libc/dns/hoststxt.h"
 #include "libc/errno.h"
-#include "libc/mem/arraylist.internal.h"
 #include "libc/runtime/runtime.h"
 #include "libc/sock/sock.h"
 #include "libc/stdio/stdio.h"

libc/dns/parseresolvconf.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/mem/arraylist.internal.h"
 #include "libc/dns/dns.h"
 #include "libc/dns/resolvconf.h"
-#include "libc/mem/arraylist.internal.h"
 #include "libc/mem/mem.h"
 #include "libc/runtime/runtime.h"
 #include "libc/sock/sock.h"

libc/dns/resolvehostsreverse.c

@@ -16,12 +16,12 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/mem/alg.h"
+#include "libc/intrin/bits.h"
 #include "libc/dns/consts.h"
 #include "libc/dns/dns.h"
 #include "libc/dns/hoststxt.h"
 #include "libc/fmt/fmt.h"
-#include "libc/intrin/bits.h"
-#include "libc/mem/alg.h"
 #include "libc/sock/sock.h"
 #include "libc/str/str.h"
 #include "libc/sysv/consts/af.h"

libc/dns/resolvehoststxt.c

@@ -16,10 +16,10 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/mem/alg.h"
 #include "libc/dns/consts.h"
 #include "libc/dns/dns.h"
 #include "libc/dns/hoststxt.h"
-#include "libc/mem/alg.h"
 #include "libc/sock/sock.h"
 #include "libc/str/str.h"
 #include "libc/sysv/consts/af.h"

libc/fmt/conv.h

@@ -17,8 +17,7 @@ COSMOPOLITAN_C_START_
 int abs(int) libcesque pureconst;
 long labs(long) libcesque pureconst;
 long long llabs(long long) libcesque pureconst;
-intmax_t imaxabs(intmax_t)
-libcesque pureconst;
+intmax_t imaxabs(intmax_t) libcesque pureconst;
 int atoi(const char *) paramsnonnull() libcesque;
 long atol(const char *) paramsnonnull() libcesque;
 long long atoll(const char *) paramsnonnull() libcesque;
@@ -45,16 +44,12 @@ size_t wcsxfrm(wchar_t *, const wchar_t *, size_t);
 ╚────────────────────────────────────────────────────────────────────────────│*/
 
 int64_t DosDateTimeToUnix(unsigned, unsigned) libcesque nosideeffect;
-struct timeval WindowsTimeToTimeVal(int64_t)
-libcesque nosideeffect;
-struct timespec WindowsTimeToTimeSpec(int64_t)
-libcesque nosideeffect;
+struct timeval WindowsTimeToTimeVal(int64_t) libcesque nosideeffect;
+struct timespec WindowsTimeToTimeSpec(int64_t) libcesque nosideeffect;
 int64_t TimeSpecToWindowsTime(struct timespec) libcesque nosideeffect;
 int64_t TimeValToWindowsTime(struct timeval) libcesque nosideeffect;
-struct timeval WindowsDurationToTimeVal(int64_t)
-libcesque nosideeffect;
-struct timespec WindowsDurationToTimeSpec(int64_t)
-libcesque nosideeffect;
+struct timeval WindowsDurationToTimeVal(int64_t) libcesque nosideeffect;
+struct timespec WindowsDurationToTimeSpec(int64_t) libcesque nosideeffect;
 
 #define MakeFileTime(x)                                        \
   ({                                                           \
@@ -124,8 +119,7 @@ imaxdiv_t imaxdiv(intmax_t, intmax_t) pureconst;
 
 #if (__GNUC__ * 100 + __GNUC_MINOR__ >= 406 || defined(__llvm__)) && \
     !defined(__STRICT_ANSI__)
-int128_t i128abs(int128_t)
-libcesque pureconst;
+int128_t i128abs(int128_t) libcesque pureconst;
 int128_t strtoi128(const char *, char **, int) paramsnonnull((1));
 uint128_t strtou128(const char *, char **, int) paramsnonnull((1));
 int128_t wcstoi128(const wchar_t *, wchar_t **, int);

libc/fmt/fmt.c

@@ -17,6 +17,7 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/fmt/fmt.h"
+
 #include "libc/assert.h"
 #include "libc/errno.h"
 #include "libc/fmt/conv.h"

libc/fmt/formatflex64.c

@@ -16,8 +16,8 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/fmt/itoa.h"
 #include "libc/intrin/popcnt.h"
+#include "libc/fmt/itoa.h"
 
 /**
  * Formats integer using decimal or hexadecimal.

libc/fmt/itoa128radix10.greg.c

@@ -16,10 +16,10 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/mem/reverse.internal.h"
 #include "libc/fmt/conv.h"
 #include "libc/fmt/itoa.h"
 #include "libc/limits.h"
-#include "libc/mem/reverse.internal.h"
 
 uint128_t __udivmodti4(uint128_t, uint128_t, uint128_t *);
 

libc/fmt/itoa64.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/mem/reverse.internal.h"
 #include "libc/fmt/conv.h"
 #include "libc/fmt/itoa.h"
-#include "libc/mem/reverse.internal.h"
 
 dontinline size_t uint64toarray(uint64_t i, char *a, int r) {
   size_t j;

libc/fmt/itoa64radix8.c

@@ -16,10 +16,10 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/mem/reverse.internal.h"
 #include "libc/fmt/conv.h"
 #include "libc/fmt/itoa.h"
 #include "libc/limits.h"
-#include "libc/mem/reverse.internal.h"
 
 /**
  * Converts unsigned 64-bit integer to octal string.

libc/integral/c.inc

@@ -756,10 +756,10 @@ typedef struct {
 #if __GNUC__ >= 6
 #pragma GCC diagnostic error "-Wnonnull-compare"
 #if defined(COSMO) && !defined(MODE_DBG) && !defined(STACK_FRAME_UNLIMITED)
-#pragma GCC diagnostic error "-Wframe-larger-than=131072"
+#pragma GCC diagnostic error "-Wframe-larger-than=16384"
 #if __GNUC__ >= 9
-// #pragma GCC diagnostic error "-Walloca-larger-than=1024"
-// #pragma GCC diagnostic error "-Wvla-larger-than=1024"
+#pragma GCC diagnostic error "-Walloca-larger-than=1024"
+#pragma GCC diagnostic error "-Wvla-larger-than=1024"
 #endif /* GCC 9+ */
 #endif /* STACK_FRAME_UNLIMITED */
 #elif __GNUC__ >= 9

libc/integral/normalize.inc

@@ -67,8 +67,10 @@
 #endif
 
 /* TODO(jart): Remove this in favor of GetStackSize() */
-#ifdef COSMO
+#if defined(COSMO) && (defined(MODE_DBG) || defined(__SANITIZE_ADDRESS__))
 #define STACKSIZE 262144 /* 256kb stack */
+#elif defined(COSMO)
+#define STACKSIZE 131072 /* 128kb stack */
 #else
 #define STACKSIZE 8388608 /* 8mb stack */
 #endif

libc/intrin/avx2intrin.internal.h

@@ -0,0 +1,133 @@
+#ifndef COSMOPOLITAN_LIBC_BITS_AVX2INTRIN_H_
+#define COSMOPOLITAN_LIBC_BITS_AVX2INTRIN_H_
+#include "libc/intrin/avxintrin.internal.h"
+#if !(__ASSEMBLER__ + __LINKER__ + 0)
+COSMOPOLITAN_C_START_
+
+#define _mm256_min_epi16(M256_0, M256_1) \
+  ((__m256i)__builtin_ia32_minps((__v16hi)(M256_0), (__v16hi)(M256_1)))
+
+/*───────────────────────────────────────────────────────────────────────────│─╗
+│ cosmopolitan § it's a trap! » avx2 » simd ops                            ─╬─│┼
+╚────────────────────────────────────────────────────────────────────────────│*/
+
+#define _mm256_add_ps(M256_0, M256_1) \
+  ((__m256)((__v8sf)(M256_0) + (__v8sf)(M256_1)))
+#define _mm256_sub_ps(M256_0, M256_1) \
+  ((__m256)((__v8sf)(M256_0) - (__v8sf)(M256_1)))
+#define _mm256_mul_ps(M256_0, M256_1) \
+  ((__m256)((__v8sf)(M256_0) * (__v8sf)(M256_1)))
+#define _mm256_div_ps(M256_0, M256_1) \
+  ((__m256)((__v8sf)(M256_0) / (__v8sf)(M256_1)))
+#define _mm256_and_ps(M256_0, M256_1) \
+  ((__m256)((__v8su)(M256_0) & (__v8su)(M256_1)))
+#define _mm256_or_ps(M256_0, M256_1) \
+  ((__m256)((__v8su)(M256_0) | (__v8su)(M256_1)))
+#define _mm256_xor_ps(M256_0, M256_1) /* XORPD [u32 simd xor] */ \
+  ((__m256)((__v8su)(M256_0) ^ (__v8su)(M256_1)))
+#define _mm256_andnot_ps(M256_0, M256_1) /* ANDNPS [u32 simd nand] */ \
+  ((__m256)(~(__v8su)(M256_0) & (__v8su)(M256_1)))
+#define _mm256_rcp_ps(M256)   __builtin_ia32_rcpps256((__v8sf)(M256))
+#define _mm256_sqrt_ps(M256)  __builtin_ia32_sqrtps256((__v8sf)(M256))
+#define _mm256_rsqrt_ps(M256) __builtin_ia32_rsqrtps256((__v8sf)(M256))
+#define _mm256_round_ps(M256, IMM) \
+  ((__m256)__builtin_ia32_roundps256((__v8sf)(__m256)(M256), IMM))
+
+#define _mm256_add_epi32(M256I_0, M256I_1) \
+  ((__m256i)((__v8su)(M256I_0) + (__v8su)(M256I_1)))
+#define _mm256_cmpgt_epi32(M256I_0, M256I_1) \
+  ((__m256i)((__v8si)(M256I_0) > (__v8si)(M256I_1)))
+#define _mm256_min_epi32(M256I_0, M256I_1) \
+  ((__m256i)__builtin_ia32_pminsd256((__v8si)(M256I_0), (__v8si)(M256I_1)))
+#define _mm256_min_epu32(M256I_0, M256I_1) \
+  ((__m256i)__builtin_ia32_pminud256((__v8si)(M256I_0), (__v8si)(M256I_1)))
+#define _mm256_max_epi32(M256I_0, M256I_1) \
+  ((__m256i)__builtin_ia32_pmaxsd256((__v8si)(M256I_0), (__v8si)(M256I_1)))
+#define _mm256_max_epu32(M256I_0, M256I_1) \
+  ((__m256i)__builtin_ia32_pmaxud256((__v8si)(M256I_0), (__v8si)(M256I_1)))
+#define _mm256_blendv_epi8(M256I_0, M256I_1, M256I_2)                          \
+  ((__m256i)__builtin_ia32_pblendvb256((__v32qi)(M256I_0), (__v32qi)(M256I_1), \
+                                       (__v32qi)(M256I_2)))
+
+#define _mm256_min_ps(M256_0, M256_1)                        \
+  ((__m256)__builtin_ia32_minps256((__v8sf)(__m256)(M256_0), \
+                                   (__v8sf)(__m256)(M256_1)))
+#define _mm256_max_ps(M256_0, M256_1)                        \
+  ((__m256)__builtin_ia32_maxps256((__v8sf)(__m256)(M256_0), \
+                                   (__v8sf)(__m256)(M256_1)))
+#define _mm256_cmpneq_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpneqps((__v8sf)(__m256)(M256_0), \
+                                   (__v8sf)(__m256)(M256_1)))
+#define _mm256_cmplt_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpltps((__v8sf)(__m256)(M256_0), \
+                                  (__v8sf)(__m256)(M256_1)))
+#define _mm256_cmpnlt_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpnltps((__v8sf)(__m256)(M256_0), \
+                                   (__v8sf)(__m256)(M256_1)))
+#define _mm256_cmple_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpleps((__v8sf)(__m256)(M256_0), \
+                                  (__v8sf)(__m256)(M256_1)))
+#define _mm256_cmpnle_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpnleps((__v8sf)(__m256)(M256_0), \
+                                   (__v8sf)(__m256)(M256_1)))
+#define _mm256_cmpgt_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpltps((__v8sf)(__m256)(M256_1), \
+                                  (__v8sf)(__m256)(M256_0)))
+#define _mm256_cmpngt_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpnltps((__v8sf)(__m256)(M256_1), \
+                                   (__v8sf)(__m256)(M256_0)))
+#define _mm256_cmpge_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpleps((__v8sf)(__m256)(M256_1), \
+                                  (__v8sf)(__m256)(M256_0)))
+#define _mm256_cmpnge_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpnleps((__v8sf)(__m256)(M256_1), \
+                                   (__v8sf)(__m256)(M256_0)))
+#define _mm256_cmpord_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpordps((__v8sf)(__m256)(M256_0), \
+                                   (__v8sf)(__m256)(M256_1)))
+#define _mm256_cmpunord_ps(M256_0, M256_1)                     \
+  ((__m256)__builtin_ia32_cmpunordps((__v8sf)(__m256)(M256_0), \
+                                     (__v8sf)(__m256)(M256_1)))
+
+/*───────────────────────────────────────────────────────────────────────────│─╗
+│ cosmopolitan § avx2 » memory ops                                         ─╬─│┼
+╚────────────────────────────────────────────────────────────────────────────│*/
+
+struct thatispacked PackedMayaliasIntyYmm {
+  __m256i Ymm;
+} mayalias;
+
+#define _mm256_set_ps(FLT_0, FLT_1, FLT_2, FLT_3, FLT_4, FLT_5, FLT_6, FLT_7) \
+  ((__m256)(__v8sf){(float)(FLT_0), (float)(FLT_1), (float)(FLT_2),           \
+                    (float)(FLT_3), (float)(FLT_4), (float)(FLT_5),           \
+                    (float)(FLT_6), (float)(FLT_7)})
+#define _mm256_set1_ps(FLT_0) \
+  _mm256_set_ps(FLT_0, FLT_0, FLT_0, FLT_0, FLT_0, FLT_0, FLT_0, FLT_0)
+#define _mm256_setr_ps(FLT_0, FLT_1, FLT_2, FLT_3, FLT_4, FLT_5, FLT_6, FLT_7) \
+  _mm256_set_ps(FLT_7, FLT_6, FLT_5, FLT_4, FLT_3, FLT_2, FLT_1, FLT_0)
+
+#define _mm256_set_epi32(INT_0, INT_1, INT_2, INT_3, INT_4, INT_5, INT_6,    \
+                         INT_7)                                              \
+  ((__m256i)(__v8si){(int)(INT_0), (int)(INT_1), (int)(INT_2), (int)(INT_3), \
+                     (int)(INT_4), (int)(INT_5), (int)(INT_6), (int)(INT_7)})
+#define _mm256_set1_epi32(INT_0) \
+  _mm256_set_epi32(INT_0, INT_0, INT_0, INT_0, INT_0, INT_0, INT_0, INT_0)
+#define _mm256_setr_epi32(INT_0, INT_1, INT_2, INT_3, INT_4, INT_5, INT_6, \
+                          INT_7)                                           \
+  _mm256_set_epi32(INT_7, INT_6, INT_5, INT_4, INT_3, INT_2, INT_1, INT_0)
+
+#define _mm256_loadu_si256(M256IP_0)            \
+  ({                                            \
+    const __m256i *Ymm = (M256IP_0);            \
+    ((struct PackedMayaliasIntyYmm *)Ymm)->Ymm; \
+  })
+
+#define _mm256_storeu_si256(M256IP_0, M256I_1)            \
+  ({                                                      \
+    __m256i *Ymm = (M256IP_0);                            \
+    ((struct PackedMayaliasIntyYmm *)Ymm)->Ymm = M256I_1; \
+  })
+
+COSMOPOLITAN_C_END_
+#endif /* !(__ASSEMBLER__ + __LINKER__ + 0) */
+#endif /* COSMOPOLITAN_LIBC_BITS_AVX2INTRIN_H_ */

libc/intrin/avxintrin.internal.h

@@ -0,0 +1,51 @@
+#ifndef COSMOPOLITAN_LIBC_BITS_AVXINTRIN_H_
+#define COSMOPOLITAN_LIBC_BITS_AVXINTRIN_H_
+#if !(__ASSEMBLER__ + __LINKER__ + 0)
+COSMOPOLITAN_C_START_
+
+typedef float __m256 _Vector_size(32) mayalias;
+typedef double __m256d _Vector_size(32) mayalias;
+typedef long long __m256i _Vector_size(32) mayalias;
+
+typedef float __m256_u _Vector_size(32) forcealign(1) mayalias;
+typedef double __m256d_u _Vector_size(32) forcealign(1) mayalias;
+typedef long long __m256i_u _Vector_size(32) forcealign(1) mayalias;
+
+typedef double __v4df _Vector_size(32);
+typedef float __v8sf _Vector_size(32);
+typedef long long __v4di _Vector_size(32);
+typedef unsigned long long __v4du _Vector_size(32);
+typedef int __v8si _Vector_size(32);
+typedef unsigned __v8su _Vector_size(32);
+typedef short __v16hi _Vector_size(32);
+typedef unsigned short __v16hu _Vector_size(32);
+typedef char __v32qi _Vector_size(32);
+typedef unsigned char __v32qu _Vector_size(32);
+
+#define _mm256_setzero_ps()       ((__m256)(__v8sf){0})
+#define _mm256_load_ps(FLOATPTR)  (*(__m256 *)(FLOATPTR))
+#define _mm256_loadu_ps(FLOATPTR) (*(__m256_u *)(FLOATPTR))
+#define _mm256_store_ps(FLOATPTR, M256_0) \
+  (*(__m256 *)(FLOATPTR) = (__m256)(M256_0))
+#define _mm256_storeu_ps(FLOATPTR, M256_0) \
+  (*(__m256_u *)(FLOATPTR) = (__m256)(M256_0))
+#define _mm256_extractf128_ps(M256_0, INT_1)                           \
+  ((__m128)__builtin_ia32_vextractf128_ps256((__v8sf)(__m256)(M256_0), \
+                                             (int)(INT_1)))
+#define _mm256_insertf128_ps(M256_0, M128_1, IMM_2) \
+  ((__m256)__builtin_ia32_vinsertf128_ps256(        \
+      (__v8sf)(__m256)(M256_0), (__v4sf)(__m128)(M128_1), (int)(IMM_2)))
+
+#ifdef __llvm__
+#define _mm256_castps128_ps256(M128_0)                                       \
+  ((__m256)__builtin_shufflevector((__v4sf)(__m128)(M128_0),                 \
+                                   (__v4sf)(__m128)(M128_0), 0, 1, 2, 3, -1, \
+                                   -1, -1, -1))
+#else
+#define _mm256_castps128_ps256(M128_0) \
+  ((__m256)__builtin_ia32_ps256_ps((__v4sf)(__m128)(M128_0)))
+#endif
+
+COSMOPOLITAN_C_END_
+#endif /* !(__ASSEMBLER__ + __LINKER__ + 0) */
+#endif /* COSMOPOLITAN_LIBC_BITS_AVXINTRIN_H_ */

libc/intrin/bits.h

@@ -15,10 +15,8 @@ uint32_t gray(uint32_t) pureconst;
 uint32_t ungray(uint32_t) pureconst;
 int _bitreverse8(int) libcesque pureconst;
 int _bitreverse16(int) libcesque pureconst;
-uint32_t _bitreverse32(uint32_t)
-libcesque pureconst;
-uint64_t _bitreverse64(uint64_t)
-libcesque pureconst;
+uint32_t _bitreverse32(uint32_t) libcesque pureconst;
+uint64_t _bitreverse64(uint64_t) libcesque pureconst;
 unsigned long _roundup2pow(unsigned long) libcesque pureconst;
 unsigned long _roundup2log(unsigned long) libcesque pureconst;
 unsigned long _rounddown2pow(unsigned long) libcesque pureconst;

libc/intrin/countbits.c

@@ -17,8 +17,8 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/assert.h"
-#include "libc/dce.h"
 #include "libc/intrin/bits.h"
+#include "libc/dce.h"
 #include "libc/nexgen32e/x86feature.h"
 
 /**

libc/intrin/createdirectory.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/files.h"
 #include "libc/nt/thunk/msabi.h"
 

libc/intrin/createfile.c

@@ -16,10 +16,10 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/nt/createfile.h"
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
+#include "libc/nt/createfile.h"
 #include "libc/nt/thunk/msabi.h"
 
 __msabi extern typeof(CreateFile) *const __imp_CreateFileW;

libc/intrin/createfilemapping.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/memory.h"
 #include "libc/nt/struct/securityattributes.h"
 #include "libc/nt/thunk/msabi.h"

libc/intrin/createfilemappingnuma.c

@@ -16,15 +16,15 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/memory.h"
 #include "libc/nt/struct/securityattributes.h"
 
-__msabi extern typeof(CreateFileMappingNuma)
-    *const __imp_CreateFileMappingNumaW;
+__msabi extern typeof(CreateFileMappingNuma) *const
+    __imp_CreateFileMappingNumaW;
 
 /**
  * Creates file mapping object on the New Technology.

libc/intrin/createnamedpipe.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/ipc.h"
 #include "libc/nt/struct/securityattributes.h"
 #include "libc/nt/thunk/msabi.h"

libc/intrin/createpipe.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/ipc.h"
 #include "libc/nt/struct/securityattributes.h"
 #include "libc/nt/thunk/msabi.h"

libc/intrin/createsymboliclink.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/files.h"
 
 __msabi extern typeof(CreateSymbolicLink) *const __imp_CreateSymbolicLinkW;

libc/intrin/cxaatexit.internal.h

@@ -1,8 +1,8 @@
 #ifndef COSMOPOLITAN_LIBC_RUNTIME_CXAATEXIT_H_
 #define COSMOPOLITAN_LIBC_RUNTIME_CXAATEXIT_H_
 #include "libc/intrin/nopl.internal.h"
-#include "libc/stdio/stdio.h"
 #include "libc/thread/tls.h"
+#include "libc/stdio/stdio.h"
 #if !(__ASSEMBLER__ + __LINKER__ + 0)
 COSMOPOLITAN_C_START_
 

libc/intrin/deletefile.c

@@ -16,8 +16,8 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/nt/files.h"
 #include "libc/nt/thunk/msabi.h"
 

libc/intrin/describerlimit.c

@@ -16,11 +16,11 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/struct/rlimit.h"
 #include "libc/dce.h"
 #include "libc/intrin/asan.internal.h"
 #include "libc/intrin/kprintf.h"
-#include "libc/intrin/strace.internal.h"
 
 const char *DescribeRlimit(char buf[64], int rc, const struct rlimit *rlim) {
   if (rc == -1) return "n/a";

libc/intrin/directmap-metal.c

@@ -17,9 +17,9 @@
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
 #include "libc/calls/calls.h"
+#include "libc/intrin/directmap.internal.h"
 #include "libc/calls/internal.h"
 #include "libc/calls/metalfile.internal.h"
-#include "libc/intrin/directmap.internal.h"
 #include "libc/macros.internal.h"
 #include "libc/runtime/pc.internal.h"
 #include "libc/str/str.h"

libc/intrin/emmintrin.internal.h

@@ -0,0 +1,244 @@
+#ifndef COSMOPOLITAN_LIBC_BITS_EMMINTRIN_H_
+#define COSMOPOLITAN_LIBC_BITS_EMMINTRIN_H_
+#include "libc/intrin/xmmintrin.internal.h"
+#if !(__ASSEMBLER__ + __LINKER__ + 0)
+
+/*───────────────────────────────────────────────────────────────────────────│─╗
+│ cosmopolitan § it's a trap! » sse2                                       ─╬─│┼
+╚────────────────────────────────────────────────────────────────────────────│*/
+
+typedef char __v16qi _Vector_size(16);
+typedef unsigned char __v16qu _Vector_size(16);
+typedef signed char __v16qs _Vector_size(16);
+
+typedef short __v8hi _Vector_size(16);
+typedef unsigned short __v8hu _Vector_size(16);
+
+typedef double __v2df _Vector_size(16);
+typedef double __m128d _Vector_size(16) forcealign(16);
+typedef double __m128d_u _Vector_size(16) forcealign(1);
+
+typedef long long __v2di _Vector_size(16);
+typedef long long __m128i _Vector_size(16) forcealign(16);
+typedef long long __m128i_u _Vector_size(16) forcealign(1);
+typedef unsigned long long __v2du _Vector_size(16);
+
+struct thatispacked mayalias __usi128ma {
+  __m128i_u __v;
+};
+
+/*───────────────────────────────────────────────────────────────────────────│─╗
+│ cosmopolitan § it's a trap! » sse2 » memory ops                          ─╬─│┼
+╚────────────────────────────────────────────────────────────────────────────│*/
+
+#define _mm_loadu_si128(M128IP) ((struct __usi128ma *)(M128IP))->__v
+#define _mm_storeu_si128(M128IP, M128I) \
+  (((struct __usi128ma *)(M128IP))->__v = (M128I))
+
+#define _mm_set_epi8(I8_15, I8_14, I8_13, I8_12, I8_11, I8_10, I8_9, I8_8,  \
+                     I8_7, I8_6, I8_5, I8_4, I8_3, I8_2, I8_1, I8_0)        \
+  ((__m128i)(__v16qi){I8_0, I8_1, I8_2, I8_3, I8_4, I8_5, I8_6, I8_7, I8_8, \
+                      I8_9, I8_10, I8_11, I8_12, I8_13, I8_14, I8_15})
+#define _mm_set_epi16(I16_7, I16_6, I16_5, I16_4, I16_3, I16_2, I16_1, I16_0) \
+  ((__m128i)(__v8hi){I16_0, I16_1, I16_2, I16_3, I16_4, I16_5, I16_6, I16_7})
+#define _mm_set_epi32(I32_3, I32_2, I32_1, I32_0) \
+  ((__m128i)(__v4si){I32_0, I32_1, I32_2, I32_3})
+#define _mm_set_epi64x(I64_1, I64_0) ((__m128i)(__v2di){I64_0, I64_1})
+
+#define _mm_setr_epi8(I8_15, I8_14, I8_13, I8_12, I8_11, I8_10, I8_9, I8_8, \
+                      I8_7, I8_6, I8_5, I8_4, I8_3, I8_2, I8_1, I8_0)       \
+  _mm_set_epi8(I8_0, I8_1, I8_2, I8_3, I8_4, I8_5, I8_6, I8_7, I8_8, I8_9,  \
+               I8_10, I8_11, I8_12, I8_13, I8_14, I8_15)
+#define _mm_setr_epi16(I16_7, I16_6, I16_5, I16_4, I16_3, I16_2, I16_1, I16_0) \
+  _mm_set_epi16(I16_0, I16_1, I16_2, I16_3, I16_4, I16_5, I16_6, I16_7)
+#define _mm_setr_epi32(I32_3, I32_2, I32_1, I32_0) \
+  _mm_set_epi32(I32_0, I32_1, I32_2, I32_3)
+#define _mm_setr_epi64x(I64_1, I64_0) _mm_set_epi64x(I64_0, I64_1)
+
+#define _mm_set1_epi8(I8) \
+  _mm_set_epi8(I8, I8, I8, I8, I8, I8, I8, I8, I8, I8, I8, I8, I8, I8, I8, I8)
+#define _mm_set1_epi16(I16) \
+  _mm_set_epi16(I16, I16, I16, I16, I16, I16, I16, I16)
+#define _mm_set1_epi32(I32)  _mm_set_epi32(I32, I32, I32, I32)
+#define _mm_set1_epi64x(I64) _mm_set_epi64x(I64, I64)
+
+#define _mm_cvtsi128_si32(M128I) ((__v4si)(M128I))[0]
+#define _mm_cvtsi32_si128(I32)   ((__m128i)(__v4si){(I32), 0, 0, 0})
+#define _mm_setzero_si128()      ((__m128i)(__v2di){0LL, 0LL})
+#define _mm_castsi128_ps(M128I)  ((__m128)(M128I))
+#define _mm_castps_si128(M128)   ((__m128i)(M128))
+#define _mm_load_si128(M128I)    (*(M128I))
+
+/*───────────────────────────────────────────────────────────────────────────│─╗
+│ cosmopolitan § it's a trap! » sse2 » simd ops                            ─╬─│┼
+╚────────────────────────────────────────────────────────────────────────────│*/
+
+#define _mm_and_si128(M128I_0, M128I_1) \
+  ((__m128i)((__v2du)(M128I_0) & (__v2du)(M128I_1)))
+#define _mm_or_si128(M128I_0, M128I_1) \
+  ((__m128i)((__v2du)(M128I_0) | (__v2du)(M128I_1)))
+#define _mm_xor_si128(M128I_0, M128I_1) \
+  ((__m128i)((__v2du)(M128I_0) ^ (__v2du)(M128I_1)))
+#define _mm_andnot_si128(M128I_0, M128I_1) \
+  ((__m128i)(~(__v2du)(M128I_0) & (__v2du)(M128I_1)))
+
+#define _mm_add_pd(M128D_0, M128D_1) \
+  (__m128d)((__v2df)(M128D_0) + (__v2df)(M128D_1))
+#define _mm_sub_pd(M128D_0, M128D_1) \
+  (__m128d)((__v2df)(M128D_0) - (__v2df)(M128D_1))
+#define _mm_mul_pd(M128D_0, M128D_1) \
+  (__m128d)((__v2df)(M128D_0) * (__v2df)(M128D_1))
+#define _mm_div_pd(M128D_0, M128D_1) \
+  (__m128d)((__v2df)(M128D_0) / (__v2df)(M128D_1))
+#define _mm_and_pd(M128D_0, M128D_1) \
+  (__m128d)((__v2df)(M128D_0) & (__v2df)(M128D_1))
+#define _mm_or_pd(M128D_0, M128D_1) \
+  (__m128d)((__v2df)(M128D_0) | (__v2df)(M128D_1))
+#define _mm_xor_pd(M128D_0, M128D_1) \
+  (__m128d)((__v2df)(M128D_0) ^ (__v2df)(M128D_1))
+#define _mm_andnot_pd(M128D_0, M128D_1) \
+  (__m128d)(~(__v2df)(M128D_0) & (__v2df)(M128D_1))
+#define _mm_sqrt_pd(M128D) __builtin_ia32_sqrtpd((__v2df)(M128D))
+
+#define _mm_min_pd(M128D_0, M128D_1) \
+  __builtin_ia32_minpd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_max_pd(M128D_0, M128D_1) \
+  __builtin_ia32_maxpd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpeq_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpeqpd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpneq_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpneqpd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmplt_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpltpd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpnlt_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpnltpd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmple_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmplepd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpnle_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpnlepd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpgt_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpltpd((__v2df)(M128D_1), (__v2df)(M128D_0))
+#define _mm_cmpngt_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpnltpd((__v2df)(M128D_1), (__v2df)(M128D_0))
+#define _mm_cmpge_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmplepd((__v2df)(M128D_1), (__v2df)(M128D_0))
+#define _mm_cmpnge_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpnlepd((__v2df)(M128D_1), (__v2df)(M128D_0))
+#define _mm_cmpord_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpordpd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpunord_pd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpunordpd((__v2df)(M128D_0), (__v2df)(M128D_1))
+
+#define _mm_sad_epu8(M128I_0, M128I_1) \
+  __builtin_ia32_psadbw128((__v16qi)(M128I_0), (__v16qi)(M128I_1))
+
+#define _mm_subs_epi8(M128I_0, M128I_1) \
+  ((__m128i)__builtin_ia32_psubsb128((__v16qi)(M128I_0), (__v16qi)(M128I_1)))
+#define _mm_subs_epu8(M128I_0, M128I_1) \
+  ((__m128i)__builtin_ia32_psubusw128((__v16qi)(M128I_0), (__v16qi)(M128I_1)))
+#define _mm_subs_epi16(M128I_0, M128I_1) \
+  ((__m128i)__builtin_ia32_psubsw128((__v8hi)(M128I_0), (__v8hi)(M128I_1)))
+#define _mm_subs_epu16(M128I_0, M128I_1) \
+  ((__m128i)__builtin_ia32_psubusw128((__v8hi)(M128I_0), (__v8hi)(M128I_1)))
+
+#define _mm_add_epi32(M128I_0, M128I_1) \
+  ((__m128i)((__v4su)(M128I_0) + (__v4su)(M128I_1)))
+#define _mm_sub_epi32(M128I_0, M128I_1) \
+  ((__m128i)((__v4su)(M128I_0) - (__v4su)(M128I_1)))
+#define _mm_madd_epi16(M128I_0, M128I_1) \
+  ((__m128i)__builtin_ia32_pmaddwd128((__v8hi)(M128I_0), (__v8hi)(M128I_1)))
+#define _mm_shuffle_epi32(V, IMM) \
+  ((__m128i)__builtin_ia32_pshufd((__v4si)(__m128i)(V), (int)(IMM)))
+
+#define _mm_slli_epi32(M128I, COUNT) \
+  ((__m128i)__builtin_ia32_pslldi128((__v4si)(M128I), (COUNT)))
+
+#define _mm_slli_si128(M128I, IMM) \
+  ((__m128i)__builtin_ia32_pslldqi128((__v2di)(__m128i)(M128I), (int)(IMM)*8))
+#define _mm_srli_si128(M128I, IMM) \
+  ((__m128i)__builtin_ia32_psrldqi128((__v2di)(__m128i)(M128I), (int)(IMM)*8))
+
+#define _mm_cmpeq_epi8(a, b) ((__m128i)((__v16qi)(a) == (__v16qi)(b)))
+#define _mm_movemask_epi8(a) __builtin_ia32_pmovmskb128((__v16qi)(a))
+
+/*───────────────────────────────────────────────────────────────────────────│─╗
+│ cosmopolitan § it's a trap! » sse2 » scalar ops                          ─╬─│┼
+╚────────────────────────────────────────────────────────────────────────────│*/
+
+#define _mm_sqrt_sd(M128D_0, M128D_1)                          \
+  ({                                                           \
+    __m128d M128d2 = __builtin_ia32_sqrtsd((__v2df)(M128D_1)); \
+    (__m128d){M128d2[0], (M128D_0)[1]};                        \
+  })
+
+#define _mm_add_sd(M128D_0, M128D_1) \
+  ({                                 \
+    (M128D_0)[0] += (M128D_1)[0];    \
+    (M128D_0);                       \
+  })
+#define _mm_sub_sd(M128D_0, M128D_1) \
+  ({                                 \
+    (M128D_0)[0] -= (M128D_1)[0];    \
+    (M128D_0);                       \
+  })
+#define _mm_mul_sd(M128D_0, M128D_1) \
+  ({                                 \
+    (M128D_0)[0] *= (M128D_1)[0];    \
+    (M128D_0);                       \
+  })
+#define _mm_div_sd(M128D_0, M128D_1) \
+  ({                                 \
+    (M128D_0)[0] /= (M128D_1)[0];    \
+    (M128D_0);                       \
+  })
+
+#define _mm_min_sd(M128D_0, M128D_1) \
+  __builtin_ia32_minsd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_max_sd(M128D_0, M128D_1) \
+  __builtin_ia32_maxsd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpeq_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpeqsd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpneq_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpneqsd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmplt_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpltsd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpnlt_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpnltsd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmple_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmplesd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpnle_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpnlesd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpgt_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpltsd((__v2df)(M128D_1), (__v2df)(M128D_0))
+#define _mm_cmpngt_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpnltsd((__v2df)(M128D_1), (__v2df)(M128D_0))
+#define _mm_cmpge_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmplesd((__v2df)(M128D_1), (__v2df)(M128D_0))
+#define _mm_cmpnge_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpnlesd((__v2df)(M128D_1), (__v2df)(M128D_0))
+#define _mm_cmpord_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpordsd((__v2df)(M128D_0), (__v2df)(M128D_1))
+#define _mm_cmpunord_sd(M128D_0, M128D_1) \
+  __builtin_ia32_cmpunordsd((__v2df)(M128D_0), (__v2df)(M128D_1))
+
+#define _mm_SSE2(op, A, B)                  \
+  ({                                        \
+    __m128i R = A;                          \
+    asm(#op " %1, %0" : "+x"(R) : "xm"(B)); \
+    R;                                      \
+  })
+#define _mm_mul_epu32(A, B)      _mm_SSE2(pmuludq, A, B)
+#define _mm_add_epi64(A, B)      _mm_SSE2(paddq, A, B)
+#define _mm_srli_epi64(A, B)     _mm_SSE2(psrlq, A, B)
+#define _mm_slli_epi64(A, B)     _mm_SSE2(psllq, A, B)
+#define _mm_unpacklo_epi64(A, B) _mm_SSE2(punpcklqdq, A, B)
+#define _mm_unpackhi_epi64(A, B) _mm_SSE2(punpckhqdq, A, B)
+
+/*───────────────────────────────────────────────────────────────────────────│─╗
+│ cosmopolitan § it's a trap! » sse2 » miscellaneous                       ─╬─│┼
+╚────────────────────────────────────────────────────────────────────────────│*/
+
+#define _mm_pause() asm("rep nop")
+
+#endif /* !(__ASSEMBLER__ + __LINKER__ + 0) */
+#endif /* COSMOPOLITAN_LIBC_BITS_EMMINTRIN_H_ */

libc/intrin/exit.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/dce.h"
 #include "libc/intrin/promises.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nexgen32e/vendor.internal.h"
 #include "libc/nt/runtime.h"
 #include "libc/runtime/runtime.h"

libc/intrin/findclose.c

@@ -16,8 +16,8 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
-#include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/strace.internal.h"
+#include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/nt/files.h"
 #include "libc/nt/thunk/msabi.h"
 

libc/intrin/findfirstfile.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/files.h"
 #include "libc/nt/memory.h"
 #include "libc/nt/struct/win32finddata.h"

libc/intrin/findnextfile.c

@@ -16,9 +16,9 @@
 │ TORTIOUS ACTION, ARISING OUT OF OR IN CONNECTION WITH THE USE OR             │
 │ PERFORMANCE OF THIS SOFTWARE.                                                │
 ╚─────────────────────────────────────────────────────────────────────────────*/
+#include "libc/intrin/strace.internal.h"
 #include "libc/calls/syscall_support-nt.internal.h"
 #include "libc/intrin/describeflags.internal.h"
-#include "libc/intrin/strace.internal.h"
 #include "libc/nt/errors.h"
 #include "libc/nt/files.h"
 #include "libc/nt/memory.h"