Commit Graph

231748 Commits

Author SHA1 Message Date
joerg
31a77d8abb Drop pointer checks that are always true. 2014-11-15 01:15:45 +00:00
jmcneill
8820e4401c Implement WSDISPLAYIO_SVIDEO, WSDISPLAYIO_GVIDEO for screen blanking 2014-11-14 23:45:02 +00:00
wiz
57a81568cf bump year 2014-11-14 22:46:34 +00:00
jmcneill
a2af6ae803 Allow the DEBE layer and output sizes to be set independently. Now you can
pass fb.margin=<n> in bootargs to add a border to the framebuffer, in case
your display doesn't let you turn off overscan and you really want to see
the whole screen.
2014-11-14 19:47:36 +00:00
maxv
833172a8e0 Do not uselessly include <sys/malloc.h>. 2014-11-14 17:34:23 +00:00
riastradh
995f5ce060 Commit to returning 1, not any nonzero value. 2014-11-14 16:43:57 +00:00
uebayasi
29c8a787f1 Tweak previous. 2014-11-14 16:29:03 +00:00
uebayasi
e0d81d86b9 Test orphan ELF section placement. 2014-11-14 16:21:12 +00:00
uebayasi
1fc7d1e960 Fix thinko in previous. 2014-11-14 16:20:42 +00:00
joerg
5e9c3bb2be Install cpuid.h on X86 and arm_neon.h on ARM. 2014-11-14 15:59:46 +00:00
joerg
f26a5b846f LLVM switched to three component point release version, so follow here. 2014-11-14 15:56:12 +00:00
joerg
f88c0f1c84 Define copysignl on !long double platforms. Be consistent in the use of
weak aliases.
2014-11-14 14:53:17 +00:00
oster
e222077349 Adjust comment to reflect reality. (5th arg, not 4th) 2014-11-14 14:45:34 +00:00
joerg
930df7c121 Fix build with clang. 2014-11-14 14:32:49 +00:00
oster
404e5f061e Fix a long-standing bug related to rebooting while a
reconstruct-to-spare is underway but not yet complete.

The issue was that a component was being marked as a used_spare when
the rebuild started, not when the rebuild was actually finished.
Marking it as a used_spare meant that the component label on the spare
was being updated such that after a reboot the component would be
considered up-to-date, regardless of whether the rebuild actually
completed!

This fix includes:
 1) Add an additional state "rf_ds_rebuilding_spare" which is used
    to denote that a spare is currently being rebuilt from the live
    components.
 2) Update the comments on the disk states, which were out-of-sync
    with reality.
 3) When rebuilding to a spare component, that spare now enters the
    state rf_ds_rebuilding_spare instead of the state rf_ds_used_spare.
 4) When the rebuild is actually complete then the spare component
    enters the rf_ds_used_spare state.  rf_ds_used_spare is now used
    exclusively for the case where the rebuilding to the spare has
    completed successfully.

XXX: Someday we need to teach raidctl(8) about this new state, and
take out the backwards compatibility code in rf_netbsdkintf.c (see
RAIDFRAME_GET_INFO in raidioctl()).  For today, this fix needs to be
generic enough that it can get backported without major grief.

XXX: Needs pullup to netbsd-5*, netbsd-6*, and netbsd-7

Fixes PR#49244.
2014-11-14 14:29:16 +00:00
uebayasi
90e9fce862 Test __start_xxx/__stop_xxx symbol generation. 2014-11-14 13:30:48 +00:00
roy
e4d839ca92 Note import of dhcpcd-6.6.2 2014-11-14 12:02:20 +00:00
roy
3c322f3bc1 Sync 2014-11-14 12:00:54 +00:00
manu
7ac57848aa Fix use-after-free on failed unmount with extended attribute enabled
When unmount failed, for instance because the mount is still busy,
UFS1 extended attributes structures were left freed while the kernel
assumes extended attributes were still enabled. This led to using
UFS1 extended attributes structures after free. With LOCKDEBUG, with
quickly triggers a panic.

The problem is fixed by:
1) clear MNT_EXTATTR flag after extended attributes structures are freed
2) attempt to restart extended attributes after failed unmount
2) set MNT_EXTATTR correctly after extended attributes restart

As a side effect, extended attribute structures are now only initialized
when extended attributes are started for the filesystem.
2014-11-14 10:09:50 +00:00
uebayasi
3dcb1bdb52 Minimal linker script test. 2014-11-14 09:03:39 +00:00
skrll
958e3256f0 IPL_SCHED -> IPL_VM
Something isn't MP safe.
2014-11-14 08:20:22 +00:00
snj
6c5df44231 mention etcupdate and reorder a bit 2014-11-14 07:06:40 +00:00
christos
8b9bd2bc1b add erfl erfcl 2014-11-14 03:31:41 +00:00
jmcneill
e409ea22ce disable hdmi and tcon before setting up the display 2014-11-14 01:05:57 +00:00
jmcneill
0f7c85b8f8 Add support for interlaced video modes. 2014-11-14 00:31:54 +00:00
snj
a421a92931 adapt to modern ISO image naming conventions 2014-11-13 22:32:53 +00:00
snj
c7e38e4844 fix tyop 2014-11-13 22:29:30 +00:00
christos
1a5ec845d4 add a couple more dummies (erf, erfc) 2014-11-13 21:43:27 +00:00
christos
8d93fd0227 move to the right offset 2014-11-13 17:46:49 +00:00
christos
299b0ec7bb fix strict aliasing violations 2014-11-13 17:19:29 +00:00
hannken
0bac62655e Change ntfs to vcache.
- Use (inumber, attrtype, attrname) as key.
- Inline ntfs_fget() and ntfs_frele() as they only get called once.
2014-11-13 16:51:53 +00:00
hannken
a26eea283a - Change ntfs_vgetex() to always load the ntnode and fnode.
- Take the vnode attributes from the NAME attribute.
- Remove now unused ntfs_times() and ntfs_filesize().
- Treat nodes without an unnamed DATA attribute as zero-sized regular files.
2014-11-13 16:51:10 +00:00
hannken
6f8e2ffe40 - Fix ntfs_ntlookupattr() to make the examples from the man page work.
- Fix ntfs_loadntnode() to always read full cluster to prevent buffer
  cache inconsistency.
- Change ntfs_vgetex() and ntfs_fget() to take a const attrname and
  always pass a possibly empty string.
- Change printf to dprintf.
- Get rid of dead fields i_next, i_prev of struct ntnode.
2014-11-13 16:49:56 +00:00
joerg
44867f9155 Adjust flags to allow building with clang. 2014-11-13 16:37:39 +00:00
tsutsui
30bc235eca Stop building a.out kernels so that mkldscript.sh is no longer necessary.
Tested "build.sh release", and the default ELF GENERIC kernel loaded by
the native bootloader just works on LUNA-II.
2014-11-13 16:18:38 +00:00
christos
cb8dda3c0e Add sysctl to selectively log arp packets from unknown network. (Adrien URBAN). 2014-11-13 16:11:18 +00:00
christos
d60f5081e2 add log_unknown_network 2014-11-13 16:10:21 +00:00
christos
039e20963e Use VAX_LABELOFFSET here; It needs to be the machine-specific one. Thanks
to gcc-4.8 for discovering the bug and to Atari for having a LABELOFFSET of
516 > 512 :-)
XXX: Perhaps we should put all those constants in <sys/bootblock.h> instead
of spreading them around.
2014-11-13 16:02:25 +00:00
uebayasi
2f06dcafd4 Revise a plan about link-set.
(I was ignorant 2 weeks ago.)
2014-11-13 15:25:48 +00:00
uebayasi
4c0e1c7bb3 Missing dependency on ldscript files. 2014-11-13 15:03:06 +00:00
uebayasi
5065266d77 `ld -r' needs ${LINKFORMAT}. This fixes the experimental config(1) modular
build for MIPS64 ports.
2014-11-13 13:44:31 +00:00
apb
7fa35347f7 regen from doc/BUILDING.mdoc revision 1.107.
This reinstates documentation for "extsrc" which was lost in 2009.
2014-11-13 08:42:35 +00:00
apb
d1f4f392c7 Document "extsrc". This was added to src/BUILDING in revision 1.90
dated 2009-11-30, but was not added to src/doc/BUILDING.mdoc,
so the changes were lost.

The original log message was:
- - - -
revision 1.90
date: 2009-11-30 16:13:22 +0000;  author: uebayasi;  state: Exp;  lines: +22 -0;
Support "extsrc", externally added programs and libraries.  Users can write
their own reach-overs, cross-build, install, and get set files just like base
and X11 / X.org.  (These sets are not included as TNF releases.)
- - - -
2014-11-13 08:25:31 +00:00
snj
62a9ce094f catch up with current ISO naming conventions 2014-11-13 08:16:42 +00:00
apb
4a6eb64432 Synchronise the "-s" part of the usage message with postinstall.
A colon-separated list of tgz files is no longer accepted; you
must use multiple -s options instead.
2014-11-13 07:11:06 +00:00
mlelstv
a735dbad97 libdm is needed by LVM early in the boot process. Fixes bin/49357. 2014-11-13 07:03:23 +00:00
uebayasi
c54b571b70 List of all link-set names. 2014-11-13 06:14:47 +00:00
christos
3cbbf4418f do the dependencies in a simpler way using a separate target 2014-11-13 02:31:24 +00:00
uebayasi
67ba08fd77 If mkldscript.sh is used to build ${PROG}, depend on it. 2014-11-13 01:09:59 +00:00
jmcneill
4de477773e On 2GB systems, we have to subtract AWIN_SDRAM_PBASE from the physical address. 2014-11-12 23:12:27 +00:00